OpenCL 无法为常量数组设置内核参数

Question

我正在尝试设置内核的参数，当我尝试设置 arg-0 时，我不断收到 CL_INVALID_ARG_SIZE，这是界限。奇怪的是，如果我只是注释掉第一个 clSetKernelArgs 其他所有似乎都可以工作。我认为这可能是常量数组的问题，除了它适用于 rand_seeds。

success = clSetKernelArg(solver_kernel, 0, sizeof(cl_float) * 10, bounds);
    if(success != CL_SUCCESS)
    {
        printf("%d\n", success);
        exit(1);
    }
    success = clSetKernelArg(solver_kernel, 1, sizeof(cl_float) * 2, seeds);
    if(success != CL_SUCCESS)
    {
        printf("%d\n", success);
        exit(1);
    }
    success = clSetKernelArg(solver_kernel, 2, sizeof(cl_int), &trials);
    if(success != CL_SUCCESS)
    {
        printf("%d\n", success);
        exit(1);
    }
    success = clSetKernelArg(solver_kernel, 3, sizeof(cl_int), &start_temp);
    if(success != CL_SUCCESS)
    {
        printf("%d\n", success);
        exit(1);
    }

这是我的内核的头文件

  __kernel void solver_kernel
    (
        __constant float bounds[10],
        __constant int rand_seeds[2],
        int trials,
        int start_temp
    )

Answer 1

来自OpenCL specification：

指定为参数值的内存对象必须是缓冲区对象 （或 NULL）如果参数被声明为内置指针或 带有__global 或__constant 限定符的用户定义类型。

所以你必须首先创建一个缓冲区并将其设置为你的内核参数。应该是这样的

cl_mem bounds_buffer = clCreateBuffer(context, CL_MEM_READ_ONLY | CL_MEM_COPY_HOST_PTR, sizeof(cl_float) * 10, bounds, &success); 
success = clSetKernelArg(solver_kernel, 0, sizeof(cl_mem), bounds_buffer);

您需要对 rand_seeds 参数执行相同的操作，即使您在这一行没有收到错误（可能是因为 sizeof(cl_float) * 2 == sizeof(cl_mem) 偶然，仍然会产生不正确的结果）。

Answer 2

如果您的缓冲区永远不会改变，您不需要使用缓冲区 + __constant 方式。这是另一种选择。

实际上有两种在内核中使用常量内存的方法：

• 使用标准缓冲区 + __constant 标志
• 使用结构参数

首选第一个（请使用@Jan 接受的答案），因为您明确说明了您希望如何处理您的数据。但在实践中，所有实现也为第二种情况使用常量内存。因为它传递给内核的数据是静态的，无论如何都不可修改。

所以，你可以像这样重写你的内核：

 typedef struct float_10 { float f[10];} float_10;
 typedef struct int_2 { int i[2];}int_2;

  __kernel void solver_kernel
    (
        float_10 bounds,
        int_2 rand_seeds,
        int trials,
        int start_temp
    )

应该具有相同的性能。

已编辑：因为您需要结构，而不是数组