来自坏 OpenCL 2.0 内核的段错误答案

【问题标题】：segfault from bad OpenCL 2.0 kernel来自坏 OpenCL 2.0 内核的段错误
【发布时间】：2015-03-13 07:39:49
【问题描述】：

我正在尝试学习 OpenCL 2.0 的新功能，并且我创建了一个小内核以尝试演示设备端入队。内核如下：

#pragma OPENCL EXTENSION cl_amd_printf : enable

__kernel void call_me(__global int *a);

__kernel void templateKernel(__global  unsigned int * output,
                         __global  unsigned int * input,
                         const     unsigned int multiplier);


__kernel void call_me(__global int *a)
{   
//do nothing
int id = get_global_id(0);
//a[id] = b[id];
}



__kernel void templateKernel(__global  unsigned int * output,
                         __global  unsigned int * input,
                         const     unsigned int multiplier)
{
uint tid = get_global_id(0);
int lid = get_local_id(0);
int gid = get_group_id(0);
int broadcast = 1;
int global_size = get_global_size(0);
if(gid == 0) {
    broadcast = work_group_broadcast(5, 0);
}
int collection = work_group_scan_exclusive_add(broadcast);  


void (^kernel_block)(void) = ^{call_me(input);};
//output[tid] = input[tid] * multiplier + collection + broadcast;
output[tid] = collection;
//output[tid] = global_size;
size_t size = 100;
//printf("hey %d\n", broadcast);
ndrange_t ndrange = ndrange_1D(size);
queue_t default_queue = get_default_queue();
/*
if(tid == 0){ 
    int status = enqueue_kernel(
        default_queue, 
        CLK_ENQUEUE_FLAGS_WAIT_KERNEL,
        ndrange,
        kernel_block            
        );
    }
*/
}

这个内核应该什么都不做，除了让它在内核中成功调用，这不会导致程序段错误。它出什么问题了？当 enqueue_kernel 调用被移除时，分段错误被移除。我的 OpenCL C 编译器设置为 --cl-std=CL2.0 并确认可以正常工作，因为广播和收集功能正常工作。

我正在使用 AMDAPPSDK 3.0 Beta。任何帮助表示赞赏。

【问题讨论】：

它甚至可以编译吗？一个典型的问题可能是您将未编译的内核传递给enqueueNDRangeKernel()，因此它是段错误，因为指针无效。在 SEG_FAULT 之前的任何 CL 调用中是否有任何错误？
我对每个 API 调用都进行了检查。他们读取状态 int。 clBuildProgram 返回正常，以及 enqueueNDRangeKernel 之前的所有其他内容。有趣的是，在这个 ubuntu 机器上，运行 watch -n 0.1 ./executable 时，没有显示构建程序状态消息。

标签： c opencl gpu

【解决方案1】：

我已经解决了我自己的问题。

问题在于，在 OpenCL 2.0 中，创建命令队列的 API 调用 clCreateCommandQueue() 已被弃用。相反，AMD 建议应该使用新的 API 调用 clCreateCommandQueueWithProperties() 来为设备端内核调用启用设备端队列。

除了使用新的 API 调用外，还必须创建至少 2 个命令队列。一个用于主机端，一个用于设备端。设备队列是在主机中创建的，使用新 API 调用附带的附加属性。

【讨论】：