0

您好，当我使用 Mac OS + OpenCL 框架时，此代码可以正常工作，但是当操作系统更改为 openSUSE 11.4 +（来自 AMD 的 OpenCL 实现）时，代码会抛出此类错误。看来 typedef float clft_complex[2]; 犯了这个错误。你能说什么呢？

错误：

Err: "/tmp/OCLRS2tPp.cl", line 4: error: kernel pointer arguments must point to
      addrSpace global, local, or constant
__kernel void linear_interp(__global clfft_complex *input,
                                                  ^

1 error detected in the compilation of "/tmp/OCLRS2tPp.cl".

Internal error: clc compiler invocation failed.

内核代码：

typedef float clfft_complex[2];

__kernel void linear_interp(__global clfft_complex *input,
                        __global clfft_complex *output)
{
    int global_id = get_global_id(0);
    input[global_id][0] = 1.5f;
    input[global_id][1] = 5.5f;
}

主机代码：

//////////////////////////////////
/* Preparing OpenCL Environment */
//////////////////////////////////

cl_uint cl_platformsN = 0;
cl_platform_id *cl_platformIDs = NULL;

clGetPlatformIDs (0, NULL, &cl_platformsN);

cl_platformIDs = (cl_platform_id*)malloc( cl_platformsN * sizeof(cl_platform_id));
clGetPlatformIDs(cl_platformsN, cl_platformIDs, NULL);

cl_int status = CL_SUCCESS;
cl_device_id device;    // Compute device
cl_context context;     // Compute context

CL_CHECK_ERROR(clGetDeviceIDs(cl_platformIDs[0], DEVICE_TYPE, 1, &device, NULL));
context = clCreateContext(NULL, 1, &device, NULL, NULL, &status);

////////////
/* Device */
////////////
cl_uint wavefronts_per_SIMD = 7;
cl_int device_max_cu;

size_t wg_count;
size_t global_work_size;

#if DEVICE_TYPE == CL_DEVICE_TYPE_GPU
    size_t local_work_size = 64;
#else
    size_t local_work_size = 1;
#endif

// Get info about the compute units on the device
CL_CHECK_ERROR(clGetDeviceInfo(device, CL_DEVICE_MAX_COMPUTE_UNITS, sizeof(cl_uint), &device_max_cu, NULL));
wg_count = device_max_cu * wavefronts_per_SIMD;


global_work_size = wg_count * local_work_size;

/////////////////////
/* Input Data Part */
/////////////////////

/* Input a slice properties */
int bits_per_sample;
int samples_per_pixel;
int theta_size;
int slice_size;

/* Read the slice */
clfft_complex *data_tiff = tiff_read_complex(tiff_input,
                                             &bits_per_sample,
                                             &samples_per_pixel,
                                             &slice_size,
                                             &theta_size);


////////////////////////
/* OpenCL - DFI Part */
////////////////////////

/* Sync events */
const int events_num = 5;
cl_event event_list[events_num];

/* Command Queue */
cl_command_queue command_queue = clCreateCommandQueue(context, device, 0, &status);

/* Program */
const char* programSource = load_program_source(KERNELS_FILE_PATH);
if(programSource == NULL) {
    fprintf(stderr, "Programm '%s' can not be created. File was not found.", KERNELS_FILE_PATH);
    return;
}

cl_program program = clCreateProgramWithSource(context, 1,
                                               (const char**)&programSource, NULL,
                                               &status);

status = clBuildProgram(program, 0, NULL, NULL, NULL, NULL);

size_t paramValueSize = 1024 * 1024, param_value_size_ret;
char *paramValue;
paramValue = (char*)calloc(paramValueSize, sizeof(char));
    status = clGetProgramBuildInfo( program,
                                device,
                                CL_PROGRAM_BUILD_LOG,
                                paramValueSize,
                                paramValue,
                                &param_value_size_ret);
printf("Err: %s", paramValue);

char buf[0x10000];
clGetProgramBuildInfo(program,
                      device,
                      CL_PROGRAM_BUILD_LOG,
                      0x10000,
                      buf,
                      NULL);

if(status != CL_SUCCESS) {
    fprintf(stderr, "Programm '%s' can not be build. (%s)", KERNELS_FILE_PATH, opencl_map_error(status));
    return;
}



/* Kernels */
cl_kernel kernel_linear_interp = clCreateKernel(program, "linear_interp", &status);
4

1 回答 1

1

首先，我不知道为什么这段代码有效，但假设你的输入是一个内核指针参数cl_mem（__global *input[2]作为参数，因为您在调用内核之前已经设置了参数的类型。（顺便说一句，你在哪里clSetKernelArg()？）

其次，你为什么要对你的输入这样做？

input[global_id][0] = 1.5f;
input[global_id][1] = 5.5f;

因为输入内存空间通常应该只是只读的..或者该内核可能只是您内核的一部分？

无论如何，我不确定你在用那个内核做什么，所以：

  1. 如果这意味着您只想要一个适用于所有输入的常量 float[2] 变量，那么您可以声明

    __constant float var[2] = {1.5f, 5.5f};

  2. 如果您的意思input实际上是您的output，并且您想在单个工作项中编写两个浮点，那么您可以将类型更改为float2，或者通过执行以下操作：

    vstore2((float2)(1.5f,5.5f), 0, input[global_id]);

    但不要忘记将本地工作项除以 2..

于 2012-06-06T15:17:53.047 回答