Необъяснимый крах CUDA

Question

У меня на компьютере выделенный графический процессор (не используется для отображения). Это свойства:

Device 0: "Tesla C2050"
CUDA Driver Version / Runtime Version          6.0 / 6.0
CUDA Capability Major/Minor version number:    2.0
Total amount of global memory:                 2688 MBytes (2818244608 bytes)
(14) Multiprocessors, ( 32) CUDA Cores/MP:     448 CUDA Cores
GPU Clock rate:                                1147 MHz (1.15 GHz)
Memory Clock rate:                             1500 Mhz
Memory Bus Width:                              384-bit
L2 Cache Size:                                 786432 bytes
Maximum Texture Dimension Size (x,y,z)         1D=(65536), 2D=(65536, 65535), 3D=(2048, 2048, 2048)
Maximum Layered 1D Texture Size, (num) layers  1D=(16384), 2048 layers
Maximum Layered 2D Texture Size, (num) layers  2D=(16384, 16384), 2048 layers
Total amount of constant memory:               65536 bytes
Total amount of shared memory per block:       49152 bytes
Total number of registers available per block: 32768
Warp size:                                     32
Maximum number of threads per multiprocessor:  1536
Maximum number of threads per block:           1024
Max dimension size of a thread block (x,y,z): (1024, 1024, 64)
Max dimension size of a grid size    (x,y,z): (65535, 65535, 65535)
Maximum memory pitch:                          2147483647 bytes
Texture alignment:                             512 bytes
Concurrent copy and kernel execution:          Yes with 2 copy engine(s)
Run time limit on kernels:                     No
Integrated GPU sharing Host Memory:            No
Support host page-locked memory mapping:       Yes
Alignment requirement for Surfaces:            Yes
Device has ECC support:                        Enabled
Device supports Unified Addressing (UVA):      Yes

Я пытаюсь запустить следующую простую программу (скопировать массив на устройство):

#include <cuda.h>
#include <curand_kernel.h>

#define N 252000 

int main( void ) {
    int a[N];
    int *dev_a;
    cudaSetDevice(0);

    cudaMalloc( (void**)&dev_a, N * sizeof(int) );
    for (long i=0; i<N; i++) {
        a[i] = 1;
    }
    cudaMemcpy( dev_a, a, N * sizeof(int), cudaMemcpyHostToDevice ); //**Crashes here**

    cudaFree( dev_a );
    cudaDeviceReset();
    return 0;
}

Если N = 251000 программа работает. Но если N = 252000 программа вылетает при cudaMemcpy(), Есть идеи, почему это может происходить?

Answer 1

Поздравляем, вы только что нашли ограничение на размер вашего стека:

int a[N];

вместо этого динамически выделите ваш хост-массив:

int *a = (int *)malloc(N*sizeof(int));

Это выделит из кучи вместо этого. Если вы будете искать в SO, вы найдете много вопросов, подобных этому, которые объясняют распределение стека и кучи и ограничения.