分离库的主机端和 CUDA 设备端版本

让我们将您的示例修改为我认为您的实际用例。修改放入一个文件中，由 进行编译，将 CUDA 代码放入一个单独的文件中，由 进行编译。这对于使双库设置正常工作非常重要;并且是有道理的，因为“main 包含需要单独编译和链接的 CUDA 内核”是编译模型的一个特殊极端情况。main().cppg++.cunvccnvcc

重构后的代码：

main.cu：

include "my_lib.hpp"

__global__ void my_kernel() {
  int z { 78 };
  int w { 90 };
  foo(&z,&w);
}

int cudamain()
{
  my_kernel<<<1,1>>>();
  return 0;
}

main.cpp：

#include <cuda_runtime_api.h>
#include "my_lib.hpp"

extern int cudamain();

int main() {
  int z { 123 };
  int w { 456 };
  foo(&z,&w);
  cudamain();
  cudaDeviceSynchronize();
  cudaDeviceReset();
}

所有其他文件仍与问题相同。

现在，构建程序所需的命令是：

c++ -c -x c++ -o my_lib-noncuda.o my_lib.cu
ar qc my_lib-noncuda.a my_lib-noncuda.o
ranlib my_lib-noncuda.a

nvcc -std=c++11 -dc -o my_lib-cuda.rdc.o my_lib.cu
ar qc my_lib-cuda.a my_lib-cuda.rdc.o
ranlib my_lib-cuda.a

# Until this line - identical to what you have tried in your question

nvcc -std=c++11 -c -rdc=true main.cu -o main.cu.o 
nvcc -dlink -o main.o main.cu.o my_lib-cuda.a

c++ -std=c++11 -o main main.cpp main.o main.cu.o -I/path/to/cuda/include \
    -L/path/to/cuda/lib64 my_lib-cuda.a my_lib-noncuda.a -lcudart -lcudadevrt

需要记住的重要一点是，在构建中需要继续执行主机端组件。因此，您必须将 CUDA 主机代码的输出传递给主链接，并且还必须将 CUDA 端库添加到主链接。否则，将缺少对代码的主机端运行时 API 支持。另请注意，必须链接设备运行时库才能实现此目的。nvcc

以下是创建两个库的方法，一个仅包含 CUDA 设备函数，另一个仅包含主机函数。 您可以省略“复杂”和警卫。但是，您的库中也会有“非 CUDA 代码”。#if#ifndefmy_lib-cuda.a

对于其他问题@talonmies请参阅社区 wiki 答案或参考我已经在评论中发布的链接：https://devblogs.nvidia.com/separate-compilation-linking-cuda-device-code/ - “高级用法：使用不同的链接器”部分。

my_lib.cu

#include "my_lib.hpp"

#ifdef __CUDA_ARCH__
__device__
#endif
#if (defined __CUDA_ARCH__) || (not defined __CUDACC__)
void foo(int*x, int* y)  { *x = *y; }
#endif

#ifndef __CUDACC__
int bar() { return 5; }
#endif

库的构建过程保持不变：（仅更改为替换现有文件，因此在不事先删除库的情况下重新构建时不会出现错误）ar qcar rc

c++ -c -x c++ -o my_lib-noncuda.o my_lib.cu
ar rc my_lib-noncuda.a my_lib-noncuda.o
ranlib my_lib-noncuda.a
nvcc -dc -o my_lib-cuda.o my_lib.cu
ar rc my_lib-cuda.a my_lib-cuda.o 
ranlib my_lib-cuda.a 

构建 CUDA 程序：（通过仅使用而不是使用简化，或者查看@talonmies社区 wiki 答案）nvccc++

nvcc -dc main.cu -o main.o
nvcc main.o my_lib-cuda.a my_lib-noncuda.a -o main

如果如上所述省略了 and in，则可以省略 的链接。my_lib-noncuda.a#if#ifndefmy_lib.cu

构建 C++ 程序：（假设 CUDA 代码周围有守卫#ifdef __CUDACC__main.cu)

c++ -x c++ -c main.cu -o main.o
c++ main.o my_lib-noncuda.a -o main