关于CUDA C 项目中“ error C2059: 语法错误:“<” ”问题的解决方法

时间：2018-02-03 16:11:32 阅读：1445 评论：0 收藏：0 [点我收藏+]

　　该问题的关键在于理解CUDA项目中C\C++文件需要由c++编译器进行编译，而CUDA C的源文件需要由CUDA的编译器nvcc.exe进行编译。

发生该语法错误的原因是cu文件被C++编译器所编译，C++编译器无法识别 “<<<”，导致报错。

为什么cu文件会被C++编译器所编译呢？原因在于我们使用#include将cu文件包含到了C++文件中。对于#include的用途，更简单的理解就是把几个文件合并成一个文件，所以，当编译C++文件中，包含其中的cu文件也会被编译，从而导致 “<<<”运算符被C++编译器编译，导致语法错误。

问题原因：不能直接把cuda程序放入cpp中去调用，即核函数的调用语句add<<<2, 128>>>(dev_a, dev_b, dev_c,size); 不能出现在 .cpp 文件中。

解决办法：可以在 .cu 文件中封装一层，就是在 .cu 文件中写一个传同样参数的核函数调用函数addKernel(int *a, int *b, int *c, int size)，即在addKernel(int *a, int *b, int *c, int size)函数中调用核函数add<<<2, 128>>>(dev_a, dev_b, dev_c,size)，然后在外边main.cpp文件中用调用普通函数的方法调用addKernel(int *a, int *b, int *c, int size)函数，此外需要在addKernel(int *a, int *b, int *c, int size)函数的定义之处和main.cpp文件头部将addKernel(int *a, int *b, int *c, int size)声明为外部函数，即需要用extern "C" 声明。这也是为什么在调用cu文件中核函数的间接调用函数addKernel(int *a, int *b, int *c, int size)时我们需要使用 extern “C”。

示例如下：

（1）创建一个CUDA 6.5 的项目，新建一个main.cpp文件，添加代码如下：

#include <stdio.h>  
#include <stdlib.h>  
//#include "kernel.cu"  
   
#define N 256
extern "C" void addKernel(int *a, int *b, int *c, int size); 

int main(int argc, char **argv)  
{  
　　int a[N];  
　　int b[N];  
　　int c[N];  
   
　　for (int i=0; i<N; i++)  
　　{  
　　　　a[i]=i;  
　　　　b[i]=2*i;  
　　　　c[i]=0;  
　　} 
　　addKernel(a, b, c, N);     
 　for(int i=0; i<N; i++)  
　　{  
　　　　printf("%d is %d.\n", i, c[i]);  
　　}  
   return 0;  
}

（2）将kernel.cu文件清空后写入下述代码：

#include "cuda_runtime.h"  
#include "device_launch_parameters.h"  
   
__global__ void add(const int *a, const int *b, int *c, int size)  
{  
　　int tid = threadIdx.x + blockIdx.x * blockDim.x;  
　　c[tid] = b[tid] + a[tid];  
}  
   
extern "C" void addKernel(const int *a, const int *b, int *c, int size)  
{  
　　int *dev_a=0;   
　　int *dev_b=0;   
　　int *dev_c=0;  
   
　　cudaSetDevice(0);  
　　cudaMalloc((void**)&dev_a, sizeof(int)*size);  
　　cudaMalloc((void**)&dev_b, sizeof(int)*size);  
　　cudaMalloc((void**)&dev_c, sizeof(int)*size);  
　　cudaMemcpy(dev_a, a, sizeof(int)*size, cudaMemcpyHostToDevice);  
　　cudaMemcpy(dev_b, b, sizeof(int)*size, cudaMemcpyHostToDevice);  
　　cudaMemcpy(dev_c, c, sizeof(int)*size, cudaMemcpyHostToDevice);  
   
　　add<<<2, 128>>>(dev_a, dev_b, dev_c,size);  
   
 　cudaMemcpy(c, dev_c, size * sizeof(int), cudaMemcpyDeviceToHost);  
   
　　cudaFree(dev_a);  
　　cudaFree(dev_b);  
　　cudaFree(dev_c);  
}