Cuda 混合 C 项目链接

Question

我有一个用 C 语言编写的大型项目，我正在尝试在其中集成一些 Cuda 内核。我正在使用“gcc -c main.c”编译我的c文件，并使用“nvcc -c cuda_GMRES.cu”编译我的.cu文件，然后我尝试使用nvcc链接这2个目标文件：“nvcc -o main.c”。 o cuda_GMRES.o”并收到以下错误：

/usr/lib/gcc/x86_64-redhat-linux/4.1.2/../../../../lib64/crt1.o：在函数中 <代码>_start'： (.text+0x20)：未定义对 main' 的引用 collect2: ld returned 1 exit status

这是我第一次尝试将 cuda 与 C 文件结合起来，我可能做错了什么。有人可以帮助我吗？我使用的是 Rocks 操作系统的 GPU 集群。

我的 main.c 文件：

#include <stdio.h>
#include <math.h> 
#include "cuda_wrapper.h"   //header containing wrapper function
//cuda_GMRES that calls the kernel   cuda_dot

int main (int argc,char* argv[])
{
//content  
//bla bla bla
//cuda Function call  
  cuda_GMRES(50); 
   return 0;
}

我的 cuda_wrapper.h 文件：

#ifndef Cuda_GMRES_cuda_wrapper_h
#define Cuda_GMRES_cuda_wrapper_h
//wrapper function declaration

void cuda_GMRES(double a);
#endif

我的 cuda_GMRES.cu 文件，包含内核调用函数：

#include <stdio.h>
#include "cuda_wrapper.h"
#include "cuda_dot.cu"   

//kernel declaration
__global__ void cuda_dot();

//kernel calling function
extern "C"
void cuda_GMRES(double a)
{
double b;

double *dev_a;
double *res;

cudaMemcpy(dev_a, &a, sizeof(double), cudaMemcpyHostToDevice );
cuda_dot<<< 1, 1 >>>(*dev_a, res );
cudaMemcpy(&b, res, sizeof(double), cudaMemcpyDeviceToHost );
}    

我的 cuda_dot.cu 文件，包含内核：

__global__ void cuda_dot(double a, double *help)
{
   *help=2*a;
}

Answer 1

您的链接命令似乎包含致命错误。假设您首先像这样编译两个对象：

gcc -c main.c
nvcc -c cuda_GMRES.cu 

您应该有两个对象文件 main.o 和 cuda_GMRES.o。然后你可以这样做：

nvcc -o main.o cuda_GMRES.o

这个命令说“使用 cuda_GMRES.o 链接一个名为 main.o 的程序文件”，即。覆盖 main.o。正是由于这个原因，链接器抱怨缺少主子例程，而您没有提供主子例程（并且您正在销毁同时包含一个主子例程的目标文件）。

您想要这样的东西：

nvcc -o executable main.o cuda_GMRES.o

其中 executable 是最终链接程序的名称，或者

nvcc main.o cuda_GMRES.o

它将发出一个名为 a.out 的默认链接程序