CUDA编程 cudaDeviceSynchronize()返回值700的意思

经过几番折腾，终于搞清了cudaDeviceSynchronize()函数同时时出错，返回值为700的原因：1、向在设备上执行的函数传递了只能在主机上使用的指针 2、越界

传错值

任何传到核函数（在设备——也就是GPU——上执行的函数）的参数都需要通过cudaMalloc()来分配内存，该函数的作用是告诉CUDA运行时在设备上分配内存。原型为

cudaMalloc((void**)ptr, size_t len);

第一个参数是一个指针，只想用于保存新分配内存地址的变量，第二个参数是分配内存的大小。除了分配内存的指针不是作为函数的返回值外，这个函数的行为与malloc()是相同的，并且返回类型为void*。

• 可以将cudaMalloc()分配的指针传递给在设备上执行的函数
• 可以在设备代码中使用cudaMalloc()分配的指针进行内存读写操作
• 可以将cudaMalloc()分配的指针传递给在主机上执行的函数
• 不能在主机代码中使用cudaMalloc()分配的指针进行内存读写操作

越界

在核函数中，要注意的是两个内置变量blockDim和gridDim。
blockDim保存的是线程块中每一维的线程数量。也就是说，threadId每个维度的数目保存在这里面
gridDim保存的是线程格中每一维的线程块数量。也就是说，blockId每个维度的数目保存在这里面
在使用的时候不要混了，否则就容易越界
tip：gridDim是二维的，而blockDim实际上是三维的