CUDA: назначение идентификатора нити в 2D сетке

Предположим, у меня есть вызов ядра с двумерной сеткой, например:

dim3 dimGrid(x, y); // not important what the actual values are
dim3 dimBlock(blockSize, blockSize);
myKernel <<< dimGrid, dimBlock >>>();

Теперь я прочитал, что многомерные сетки просто предназначены для облегчения программирования — базовое оборудование будет когда-либо использовать только 1D линейно кэшированную память (если вы не используете текстурную память, но это здесь не актуально).

Мой вопрос: в каком порядке потоки будут назначаться индексам сетки во время планирования деформации? Будут ли они назначены горизонтально («повторять» x, затем y) или вертикально («повторять» y, затем x)? Это может быть важно для улучшения объединения памяти, в зависимости от того, как я обращаюсь к своей памяти в ядре.

Чтобы сделать это более понятным, предположим, что следующее представляет идентификаторы потока применительно к моей (воображаемой) сетке с «горизонтальным» распределением:

[ 0  1  2  3 ]
[ 4  5  6  7 ]
[ 8  9 10 11 ]
[ ...        ]

И «вертикальное» распределение будет:

[ 0  4  8 .. ]
[ 1  5  9 .. ]
[ 2  6 10 .. ]
[ 3  7 11 .. ]

Я надеюсь, что вы можете увидеть, как это может повлиять на объединение: в каждом варианте будет определенный оптимальный способ доступа к буферу памяти моего устройства.

К сожалению, я не нашел никакой подробной информации по этому вопросу ..