我正在尝试遵循https://docs.nvidia.com/cuda/cuda-c-programming-guide/index.html的B.12部分进行原子添加，它适用于浮点数。简单地从那里复制和粘贴代码并将类型更改为浮点数是行不通的，因为我不能执行从全局到私有的指针强制转换，这是atomicCAS操作所必需的。为了克服这个问题，我决定使用atomic_xchg()，因为它使用浮点数，并
浏览 137提问于2019-03-23得票数 1
在CUDA编程中，原子函数(如atomic_add)被广泛用于计数或执行求和/聚合。但是，与普通全局内存读写相比，我找不到有关原子函数速度的信息。考虑以下任务，其中我们想要计算一个包含256 K元素的浮点数组。每个元素是超过1000个中间变量的和，这是首先计算的。一种方法是使用atomic_add；另一种方法是对中间结果使用一个256 K*1000临时数组，然后减少这个数组(通过求和)。
第一种方法使用原子
浏览 7提问于2021-04-02得票数 0
回答已采纳
我正在编写用于稀疏矩阵运算的OpenCL代码，我发现当包含内核的代码执行一两次时，它就能正常工作。但每运行几次，答案就会略有偏差。下面是我使用的非常简单的内核： __global int * JA,IBGN; ii <= IEND; ii++) Y[IA[ii]-1] += A[ii]*X[ICOL];
浏览 1提问于2012-11-03得票数 3
我的系统是debian 10，我想实现原子操作，但我发现没有用于原子操作的头文件和API函数。你怎么了？原子操作不是内核级别的函数吗？为什么不行？directory ^~~~~~~~~~~~~~
compilation terminated. man原子API错误： # man atomic_addNo manual entry for atomic_add
浏览 410提问于2021-08-21得票数 1
回答已采纳
1回答
我正在对OpenCL使用原子操作。相同的代码在英特尔CPU上工作正常，但在Nvidia GPU上出现错误。我已经启用了32位和64位的原子。int cidx=idx%10;
C[idx]=In1[idx] & In2[idx];这只是整体代码的一部分。它给出了构建错误“不支持的操作”，而运行在Nvidia Quadro GPU上，而它在英特尔i3，至强和AMD处理器上都工作得很好。
浏览 0提问于2012-10-18得票数 2
1回答
regs_return_value(regs) == 0) { }}
我担心另一个重命名的syscall可能会在j探针之后出现当前的preempt1，并且我会发送不正确的返回代码和参数。但是，这是否意味着中断在整个链中是禁用的(j探针、->、->、kret探头)，还是仅用于单个k探头？
浏览 2提问于2016-10-03得票数 7
回答已采纳
我写了我的atomic_inc，用于使用asm递增一个整数，它实际上是用于共享对象的引用计数。gcc 4.8.2 -fsanitize=thread报告了数据竞争，我最终发现可能是我的atomic_inc引起的。我不相信我的代码有一个与数据竞争有关的bug，这是不是由tsan误报的？static inline int atomic_add(volatile int *count, int add) {
__asm__ __vo
浏览 0提问于2016-03-21得票数 2
我对基于Linux内核的C编码风格非常陌生.我试图从"arch/arm64/include/asm/atomic.h“文件(的第112-124行)了解”“函数的以下实现。static inline void atomic_add(int i, atomic_t *v) unsigned long tmp; asm volatile("// atomic_add</e
浏览 6提问于2021-04-27得票数 0
回答已采纳
2回答
我对gcc的在线装配很陌生。为什么这个代码输出"1“而不是"5"？代码：static inline int atomic_add(volatile int *mem, int add) asm volatile("memory" return add;{ int b=5;
printf ( "%d\n", atomic
浏览 1提问于2015-03-08得票数 1
回答已采纳
我需要从float中的多个线程中向相同的全局内存地址添加一个OpenCL。对于任何两次模拟运行，结果从来都不是相同的，对atomic_add_f函数的调用是此错误的根源。我正在使用带驱动程序436.02的Nvidia泰坦Xp GPU。由于OpenCL不支持使用float的atomic_add，所以有使用atomic_cmpxchg的
void atomic_add_f(volati
浏览 6提问于2019-08-30得票数 2
回答已采纳
2回答
我知道我可以通过使用过滤器floatformat:2来限制浮动中的小数，它输出一个局部浮点数，我也知道过滤器stringformat:"f"，它输出像1.54这样的虚线浮点数，而不是像1,54那样的局部逗号浮点数例如，如果原始浮点数为1.54233，则我希望打印1.54，而不是1,54或1.54233。在不需要自定义过滤器的情况下，能实现这一点吗？
浏览 5提问于2015-12-11得票数 8
回答已采纳
const uint i = get_global_id(0); sum[map[i]] += 12.34;}这个能行吗？"+=“是以原子方式实现的，还是存在并发操作相互覆盖的可
浏览 3提问于2015-03-04得票数 0
回答已采纳
根据 41 { 43int result; 45 prefetchw(&v->counter);
46 __asm__ __volatile__("@ atomic_add\n
浏览 1提问于2014-05-19得票数 1
1回答
我开始在内核中对__global int* vnumber缓冲区使用atom_add操作：atom_add(&vnumber[0], 1);。这显然给了我错误的结果。因此，作为额外的检查，我将add指令移到了内核的开头，以便为每个线程执行该指令。当使用512x512线程启动内核时，vnumber[0]的内容是：524288，它恰好是2x512x512，是我应该得到的值的两倍。有趣的是，通过将add操作更改为atom_add(&
浏览 1提问于2011-11-02得票数 4
回答已采纳
我试图通过识别三维体积位置和组ID来计算每个组的局部和。 local_sum= 0;
int local_offset = atomic_add(&local_sum, src[id]);
浏览 4提问于2017-04-10得票数 0
回答已采纳
3回答
我似乎有一个损坏的堆，我不知道为什么会发生这种情况...==12697== at 0xDD0725: __gnu_cxx::__atomic_add(int如果需要进一步的调试，请让我知道源代码。这是测试了一些东西，我将它们插入到通过引用传递的向量的副本中。
干杯!
浏览 3提问于2010-12-03得票数 0
回答已采纳
然后，它输出两个列表；即发现位于线A之外的所有点的集合A，反之亦然。作为另一种选择，我测试了在内核中保留一个全局索引，记录哪些点与哪一行相关。在每次迭代期间，整个集合中每个点的索引被切换为0(无线)、A或B等(即相关线id)。在随后的迭代中，只有索引与在该周期中被检查的'live‘集合匹配的</em
浏览 1提问于2015-08-03得票数 0
假设我正在使用一个自定义GLSL着色器，它使用由11个浮点数组成的特殊交错数组格式:位置(3个浮点数)，正常(3个浮点数)，UVcoord-1 (2个浮点数)，UVcoord-2 (2个浮点数)，自定义属性(1个浮点数)。Blender、Maya等)，然后将其导入我的应用程序。我已经在网上找遍了，我似乎找不到一种允许每个vertex.Am有多个(自定义)数据通道<
浏览 1提问于2011-01-25得票数 1
回答已采纳
云服务器
ICP备案
实时音视频
即时通信 IM
对象存储
腾讯云开发者
