如何在 C 中将向量参数传递给 OpenCL 内核？

Question

我在将向量类型 (uint8) 参数从 C 中的主机代码传递给 OpenCL 内核函数时遇到问题。

在主机中我有一个数组中的数据：

cl_uint dataArr[8] = { 1, 2, 3, 4, 5, 6, 7, 8 };

（我的真实数据不仅仅是[1, 8]；这只是为了便于解释。）

然后我将数据传输到缓冲区以传递给内核：

cl_mem kernelInputData = clCreateBuffer(context,
    CL_MEM_READ_ONLY | CL_MEM_COPY_HOST_PTR, sizeof(cl_uint)*8, dataArr, NULL);

接下来，我将这个缓冲区传递给内核：

clSetKernelArg(kernel, 0, sizeof(cl_mem), &kernelInputData);

内核函数的签名看起来像这样：

kernel void kernelFunction(constant uint8 *vectorPtr)

但是，内核似乎没有从指向kernelInputData 的指针中获取正确的输入数据。当我从内核中传回值时，我看到vectorPtr 指向具有这种结构的东西：( 1, 2, 3, 4, 5, ?, ?, ? ) 其中问号通常是4293848814，但有时是0。无论哪种方式，都不是他们应该的样子。

我做错了什么？

---

编辑：

我已经从使用数组切换到主机端的 cl_uint8。我现在有：

cl_uint8 dataVector = { 1, 2, 3, 4, 5, 6, 7, 8 };

然后我像这样将这个向量传递给内核：

clSetKernelArg(kernel, 0, sizeof(cl_uint8), &dataVector);

内核函数的签名看起来像这样：

kernel void kernelFunction(constant uint8 *vectorPtr)

但是，运行此代码会在clSetKernelArg() 上给我一个CL_INVALID_ARG_SIZE 错误。如果我将ARG_SIZE 参数切换为sizeof(cl_uint8 *)，则此错误消失，但随后我在__dynamic_cast 中的clSetKernelArg() 中收到EXC_BAD_ACCESS 错误。

我的设备是：

Apple Macbook Pro（2009 年中）
OSX 10.8 山狮
NVIDIA GeForce 9400M
OpenCL 1.0
CLH 1.0

Answer 1

您正在定义一个大小为 8 的 cl_uint 数组。 cl_mem 的创建和内核参数的设置是正确的。 但是您的内核参数不正确：您尝试读取 cl_uint8 数组而不是 cl_uint。

如果要使用向量数据类型，必须声明：cl_uint8 dataArr of size 1。 或者，如果您想使用大小为 8 的数组：kernel void kernelFunction(constant uint *vectorPtr, uint size):

编辑：

cl_uint8 dataVector 的内核参数不是指针。 所以，正确的代码是：

cl_uint8 dataVector = { 1, 2, 3, 4, 5, 6, 7, 8 };
clSetKernelArg(kernel, 0, sizeof(cl_uint8), &dataVector);

和

kernel void kernelFunction(constant uint8 vectorPtr)

Answer 2

最小可运行示例

int2 被传递给内核。它最初被创建为cl_int 的数组。

#include <assert.h>
#include <stdlib.h>

#include <CL/cl.h>

int main(void) {
    const char *source =
        "__kernel void main(__global int2 *out) {\n"
        "      out[get_global_id(0)]++;\n"
        "}\n";
    cl_command_queue command_queue;
    cl_context context;
    cl_device_id device;
    cl_int input[] = {0, 1, 2, 3};
    const size_t global_work_size = sizeof(input) / sizeof(cl_int2);
    cl_kernel kernel;
    cl_mem buffer;
    cl_platform_id platform;
    cl_program program;

    clGetPlatformIDs(1, &platform, NULL);
    clGetDeviceIDs(platform, CL_DEVICE_TYPE_ALL, 1, &device, NULL);
    context = clCreateContext(NULL, 1, &device, NULL, NULL, NULL);
    command_queue = clCreateCommandQueue(context, device, 0, NULL);
    buffer = clCreateBuffer(context, CL_MEM_READ_WRITE | CL_MEM_COPY_HOST_PTR, sizeof(input), &input, NULL);
    program = clCreateProgramWithSource(context, 1, &source, NULL, NULL);
    clBuildProgram(program, 1, &device, "", NULL, NULL);
    kernel = clCreateKernel(program, "main", NULL);
    clSetKernelArg(kernel, 0, sizeof(cl_mem), &buffer);
    clEnqueueNDRangeKernel(command_queue, kernel, 1, NULL, &global_work_size, NULL, 0, NULL, NULL);
    clFlush(command_queue);
    clFinish(command_queue);
    clEnqueueReadBuffer(command_queue, buffer, CL_TRUE, 0, sizeof(input), &input, 0, NULL, NULL);

    assert(input[0] == 1);
    assert(input[1] == 2);
    assert(input[2] == 3);
    assert(input[3] == 4);
    return EXIT_SUCCESS;
}

在 Ubuntu 15.10 OpenCL 1.2 NVIDIA 352.53 上测试。