设置（标量）内核参数 OpenCL 后的值错误

Question

我正在开发一个 OpenCL 程序，但每次执行的输出都不同。我认为这与将参数传递给内核有关，因为当我对特定执行的值进行硬编码时，每次执行后的输出都是相似的。

我的内核是这样的：

__kernel void sample_kernel(__global double *BufferA, int scalar1, int scalar2, int scalar3, ...) {

    for(int i = -1*scalar1; i < scalar1; i++) {
        for(int j = -1*scalar1; j < scalar1, j++) {
            if(scalar2 > 0 && scalar3 > 0) // do something.
        }
    }
}

这就是我设置内核参数的方式：

int scalar1 = 1;
int scalar2 = 2;
int scalar3 = 3;

Samplekernel.setArg(0, d_BufferA);
Samplekernel.setArg(1, sizeof(int), &scalar1);
Samplekernel.setArg(2, sizeof(int), &scalar2);
Samplekernel.setArg(3, sizeof(int), &scalar3);

奇怪的是，当我添加...

if(scalar1 != 1) scalar1 = 1;
if(scalar2 != 2) scalar2 = 2;
if(scalar3 != 3) scalar3 = 3;

...在双for循环之前的内核中，输出是正确的。

我在 Nvidia K20m GPU、OpenCL 1.1 版上运行我的程序。当我在 Nvidia C2075 上运行我的代码时，一切似乎都运行良好......

有人知道问题可能是什么吗？看起来该值未正确复制或被覆盖，但我没有在 for 循环之前访问该值...

提前致谢！

Answer 1

我看起来你正在将一个指向 int 的指针传递给 setArg

Samplekernel.setArg(1, sizeof(int), &scalar1);

然后，在你的内核参数列表中，你有整数值，而不是指针：

__kernel void sample_kernel(__global double *BufferA, int scalar1, ...

您可以在内核参数列表中使用指针，如下所示：

__kernel void sample_kernel(__global double *BufferA, global int *scalar1,

或者 - 这就是我的建议，因为我在 C++ 绑定规范中找不到您的 kernel.setArg (...) 版本，但由于某种原因只能在 khronos.org 上的实现中找到 - 直接复制像这样的标量：

Samplekernel.setArg(1, scalar1);

这还有一个优点，即变量在内核的私有内存空间中可用，而不是在全局空间中，就像您将缓冲区指定为参数时一样。

您使用的 Kernel::setArg 版本可能不会复制该值，但可能仅用于主机绑定内核，但我不同意。

另外，您可能需要检查 setArg 的返回值是否有错误。