我想测试一下CUDA kernel函数中的for循环的循环次数可不可以无限大。于是我写了一个简单的代码如下:
于是当size像下面的一千万那么大的时候,程序不正确了。显示调用核函数失败 unspecific launch failure
我用nsight带的工具测试了一下,并不是寄存器超了或者内存分配失败或溢出,只是随着size的增加,每个warp的指令数IPW(Instructions Per Warp)会增加。是不是错误与这个有关?但是下面的程序代码看起来没有什么错误,如果换成C++的话循环多少次都可以,是不是CUDA对kernel有什么限制?我想知道它错误的原因。
系统:Win10 pro 64bit
IDE:Visual Studio 2015 community
CUDA 8.0
GPU: GTX860M 4GB
#include "cuda_runtime.h"
#include "device_launch_parameters.h"
#include "stdlib.h"
#include
using namespace std;
global void Kernel(double *M_gpu, int size)
{
for (int i = 0; i < size; i++)
{
M_gpu[i] = i / 2 + 6;
}
}
int main()
{
cudaError_t cudaStatus;
//分配CPU空间
int size = 10000000;
double M = (double *)malloc(sizeof(double)*size);
//分配GPU空间
double *M_gpu;
cudaStatus = cudaMalloc((void*)&M_gpu, sizeof(double)*size);
if (cudaStatus != cudaSuccess)
{
cout << "分配CPU空间失败!" << cudaGetErrorString(cudaStatus) << endl; getchar(); exit(0);
}
//调用核函数
Kernel << > > (M_gpu, size);
cudaDeviceSynchronize();
cudaStatus = cudaGetLastError();
if (cudaStatus != cudaSuccess)
{
cout << "调用核函数失败!" << cudaGetErrorString(cudaStatus) << endl; getchar(); exit(0);
}
//将数据从GPU拷贝回CPU
cudaStatus = cudaMemcpy(M, M_gpu, sizeof(double)*size, cudaMemcpyDeviceToHost);
if (cudaStatus != cudaSuccess)
{
cout << "拷贝数据失败!" << cudaGetErrorString(cudaStatus) << endl; getchar(); exit(0);
}
//END
cout << "Success!" << endl;
getchar();
}