장벽을 사용하면 CL_INVALID_WORK_GROUP_SIZE 오류가 발생합니다.

Question

내 커널에서 장벽을 사용하면 (CLK_LOCAL_MEM_FENCE 또는 CLK_GLOBAL_MEM_FENCE) CL_INVALID_WORK_GROUP_SIZE 오류가 발생합니다. 전역 작업 크기는 512이고 로컬 작업 크기는 128이며 65536 항목을 계산해야하며 장치의 최대 작업 그룹 크기는 1024이며 한 차원 만 사용하고 있습니다. Java 바인딩의 경우 JOCL을 사용합니다. 커널은 매우 간단합니다 :

kernel void sum(global float *input, global float *output, const int numElements, local float *localCopy 
{ 
    localCopy[get_local_id(0)] = grid[get_global_id(0)]; 
    barrier(CLK_LOCAL_MEM_FENCE); // or barrier(CLK_GLOBAL_MEM_FENCE) 
} 

나는 Intel(R) Xeon(R) CPU X5570 @ 2.93GHz에 커널을 실행하고 오픈 CL 1.2을 사용할 수 있습니다. 호출하는 방법은

kernel.putArg(aCLBuffer).putArg(bCLBuffer).putArg(elementCount).putNullArg(localWorkSize); 
queue.put1DRangeKernel(kernel, 0, globalWorkSize, localWorkSize); 

처럼 보이지만 오류가 항상 동일합니다 : 내가 잘못 뭐하는 거지

[...]can not enqueue 1DRange CLKernel [...] with gwo: null gws: {512} lws: {128} 
cond.: null events: null [error: CL_INVALID_WORK_GROUP_SIZE] 

?

Answer 1

일부 OpenCL 플랫폼에서 예상되는 동작입니다. 예를 들어 Apple 시스템에서 CPU 장치의 최대 작업 그룹 크기는 1024입니다. 그러나 커널에 장벽이있는 경우 해당 특정 커널의 최대 작업 그룹 크기는 1로 줄어 듭니다.

CL_KERNEL_WORK_GROUP_SIZE 매개 변수와 함께 clGetKernelWorkGroupInfo 함수를 사용하여 특정 커널의 최대 작업 그룹 크기를 쿼리 할 수 ​​있습니다. 반환 된 값은 clGetDeviceInfo 및 CL_DEVICE_MAX_WORK_GROUP_SIZE에 의해 반환 된 값을 넘지 않지만이 경우처럼 작게 허용됩니다.