OpenCL 세마포에서 교착 상태를 어떻게 막을 수 있습니까?

Question

나는 세마포어를 만드는 방법에 대한 마지막 예제를 제외하고는 위의 모든 튜토리얼을 수행하고있다. 논리는 꽤 간단하지만 왜이 커널이 무한 루프를 일으키는 지 알 수 없습니다.

myKernel.cl

#pragma OPENCL EXTENSION cl_khr_global_int32_base_atomics : enable 
void GetSemaphor(__global int * semaphor, __global int * data) { 
    int occupied = atom_xchg(semaphor, 1); 
    int realityCheck = 0; 
    while(occupied == 1 && realityCheck++ < 100000) 
     occupied = atom_xchg(semaphor, 1); 
} 

void ReleaseSemaphor(__global int * semaphor) 
{ 
    int prevVal = atom_xchg(semaphor, 0); 
} 

__kernel void myKernel(__global int* data, __global int* semaphor) 
{ 
    // semaphor[0] is set to 0 on the host. 
    GetSemaphor(&semaphor[0], data); 
    data[0]++; 
    ReleaseSemaphor(&semaphor[0]); 
} 

이 함께 :

* cl_khr_global_int32_base_atomics CL을 갖는 쿼드 NVS (290)에

오픈 CL 1.2

FULL_PROFILE

_khr_global_int32_extended_atomics

Answer 1

본 튜토리얼은 틀렸고 GPU 장치에서는 작동하지 않습니다. HW arquitecture로 인해.

작업 그룹 내의 작업 항목을 차단하는 모든 종류의 동기화 메커니즘이 작동하지 않습니다. 블로킹 상태는 전체 작업 그룹에 영향을 미치므로 무한 루프가 발생합니다.

작업 그룹 크기가 1 인 경우에만 또는 작업 그룹을 통해 수행 할 수 있습니다.