OpenCL NDRange用法-内核仅更改输出缓冲区的一部分

库特施凯姆

我有一个用3维NDRange调用的内核,但它只更改输出缓冲区的一部分。

核心:

__kernel void Kernel2(
 __global const float* K2BufIn,
 __global float* K2BufOut)
{

    int id0 = get_global_id(0);
    int id1 = get_global_id(1);
    int id2 = get_global_id(2);
    int gs0=get_global_size(0);
    int gs1=get_global_size(1);
    int gs2=get_global_size(2);
    int globalThreadNum = id0 + id1 * gs0 + id2 * gs0 * gs1;

    K2BufOut[globalThreadNum] = K2BufIn[globalThreadNum] * K2BufIn[globalThreadNum];

}

这称为:

float pK2BufInData[24] = {1.0, 2.0, 3.0, 4.0, 5.0, 6.0, 7.0, 8.0, 9.0, 10.0, 11.0, 12.0, 13.0, 14.0, 15.0, 16.0, 17.0, 18.0, 19.0, 20.0, 21.0, 22.0, 23.0, 24.0};
float pK2BufOutData[24] = {};
int sizeK2BufIn = 24;
int sizeK2BufOut = 24;

K2BufIn = cl::Buffer(context_, CL_MEM_READ_WRITE, sizeK2BufIn);
K2BufOut = cl::Buffer(context_, CL_MEM_READ_WRITE, sizeK2BufOut);

commandQ_.enqueueWriteBuffer(K2BufIn, CL_TRUE, 0, sizeK2BufIn, pK2BufInData);

kernel_Kernel2_.setArg(0, K2BufIn);
kernel_Kernel2_.setArg(1, K2BufOut);


commandQ_.enqueueNDRangeKernel(kernel_Kernel2_, cl::NULLRange, cl::NDRange(4,3,2));

commandQ_.enqueueReadBuffer(K2BufOut, CL_TRUE, 0, sizeK2BufOut, pK2BufOutData);

我期望的是pK2BufOutData然后包含输入数字的平方。但是,调试给了我:

(gdb) p *[email protected]
$17 = {0 <repeats 16 times>, 289, 324, 361, 400, 441, 484, 529, 576}

这意味着该代码仅适用于最后8个条目。怎么了

库特施凯姆

我在此线程中找到了答案:get_global_id(1)问题;

事实证明这条线

commandQ_.enqueueNDRangeKernel(kernel_Kernel2_, cl::NULLRange, cl::NDRange(4,3,2));

必须更改为

commandQ_.enqueueNDRangeKernel(kernel_Kernel2_, cl::NDRange(), cl::NDRange(4,3,2));

本文收集自互联网,转载请注明来源。

如有侵权,请联系 [email protected] 删除。

编辑于
0

我来说两句

0 条评论
登录 后参与评论

相关文章