__syncthreads () тупик

Question

Будет ли __syncthreads () вызывать мертвую блокировку, если ее выполняют только несколько потоков?

У меня есть такое ядро:

__global__ void Kernel(int N,int *a)
{
    if(threadIdx.x<N)
    {
      for(int i=0;i<N;i++)
       {
        a[threadIdx.x]= //Some calculation using a and i
        __syncthreads()
       }
    }
}

если число потоков в блоке больше N, то некоторые потоки не будут выполнять код. это приведет к тупику?
если да, то как я могу изменить код?

Answer 1

Вы должны не использовать __syncthreads() в расходящемся коде. Его поведение в таких обстоятельствах не определено.

__syncthreads() может появляться в условной ветви только в том случае, если вы уверены, что эта ветвь будет одинаково оценена одинаково всеми потоками в блоке (либо все, либо никакие потоки из блока не принимают ветвь) .

Answer 2

Технически ядра не могут тупиковать; они могут только тайм-аут. Но да, то, что вы описываете, реально и может произойти. Эта проблема уже обсуждалась ранее, например: Пример реалистичного тупика в CUDA / OpenCL