“__kernel”不命名类型

Question

我正在尝试编译在这里找到的代码：http://developer.amd.com/tools-and-sdks/opencl-zone/opencl-resources/introductory-tutorial-to-opencl/

我正在使用以下命令编译它：

g++ -Wall -O2 -lm -lOpenCL -g -Wno-unknown-pragmas foo.cpp -o foo

导致问题的代码部分如下：

#pragma OPENCL EXTENSION cl_khr_byte_addressable_store : enable
 __constant char hw[] = "Hello World\n";

 __kernel void hello(__global char * out) {
      size_t tid = get_global_id(0);
      out[tid] = hw[tid];
}

我得到以下错误：

foo.cpp:105:2: error: ‘__constant’ does not name a type
  __constant char hw[] = "Hello World\n";

foo.cpp:107:2: error: ‘__kernel’ does not name a type
  __kernel void hello(__global char * out) {

有人能解释一下为什么会发生这种情况吗？标题与链接上的内容完全相同。

谢谢

Answer 1

你不能像那样编译OpenCL代码(没有更多的支持基础设施，比如支持OpenCL的编译器和用于OpenCL功能的库-- Clang能够为x86编译OpenCL，但是当它试图链接东西时，却抱怨没有支持库)。

典型的OpenCL应用程序如下所示：

// Get platform, device and context - this is about 10-20 lines of "boilerplate" code. 
const char* source = "... your code goes here ...";
// But you could of course read it from a file, for example!
cl_int err;
clProgram prog = clCreateProgramWithSource(context, 1, &source, NULL, &err);
err = clBuildProgram(prog, 1, &device, NULL, NULL, NULL);
cl_kernel kern = clCreateKernel(prog, "hello", &err);
cl_mem out = clCreateBuffer(context, CL_MEM_READ_WRITE, 100, NULL, err);
err = clSetKernelArg(kernel, 0, sizeof(out), out);
size_t range = 1;
cl_command_queue queue = cl_create_command_queue( ... );
cl_event event;
err = clEnqueueNDRange(queue, kern, 1, NULL, &size, NULL, 0, NULL, &event);
clFlush(queue);
clWaitForEvent(event);
// Lots of lines of code to release everything. 

我刚刚手写了上面的几行代码-我家里没有CL环境，所以我无法检查它-它显示了一般原理，我跳过了相当多的设置/拆卸代码-当然，应该为每次对OpenCL库的调用执行错误检查，因为它通常很容易出错并返回错误，这会导致下一步崩溃/出错

有一些面向对象的变体，它允许您避免一些清理工作(析构函数为您做这件事)，但由于我只编写了几次这样的代码，而不是上面所示的基本C版本，所以我必须查看文档或查看我在工作中使用的"OpenCL C++ bindings card“。

Answer 2

我在同一教程中遇到了同样的问题。这是我克服它的尝试。

本教程令人困惑的地方在于，它只给出了OpenCL代码，而没有显式地告诉您将该代码放在名为"lesson1_kernel.cl“的文件中

我之所以弄明白这一点，是因为在本教程的前面，本机代码读取了这个文件：

std::ifstream file("lesson1_kernels.cl");
checkErr(file.is_open() ? CL_SUCCESS:-1, "lesson1_kernel.cl");
std::string prog(
    std::istreambuf_iterator<char>(file),
    (std::istreambuf_iterator<char>()));
cl::Program::Sources source(
    1,
    std::make_pair(prog.c_str(), prog.length()+1));

该教程中以前的所有“本机代码”都属于您将要编译的文件。根据本教程的说明，本机代码属于一个名为“esson1.cpp”的文件。

gcc –o hello_world –Ipath-OpenCL-include –Lpath-OpenCL-libdir lesson1.cpp –lOpenCL

我不想为这样一个简单的一次性脚本创建一个新的lesson1_kernels.cl文件，所以我将所有的OpenCL代码放入一个字符串中，并使用该字符串使用适当的转义字符创建了cl::Program::Sources对象：

const std::string openCLCode("#pragma OPENCL EXTENSION cl_khr_byte_addressable_store : enable\n__constant char hw[] = \"Hello World\\n\";\n__kernel void hello(__global char * out) \n\n{\n  size_t tid = get_global_id(0);\n  out[tid] = hw[tid];\n}\n");

和：

cl::Program::Sources source(
    1,
    std::make_pair(openCLCode.c_str(), openCLCode.length()+1));
cl::Program program(context, source);

一旦我这样做了，我就能够编译和运行程序，没有更多的问题。感谢theNoobProgrammer发布我的问题，并感谢Matts Petersson帮助我解决了这个问题，而不需要对教程代码进行重大修改。