Windows下NVCC错误信息与编译代码的名称修饰是否存在差异？

问题本质 #

你遇到的是CUDA设备函数与MSVC主机函数的名称修饰规则不兼容导致的链接错误，和Dependency Walker的显示逻辑无关：

• 错误信息中的_ZN7ustructaSERKS_是NVCC对CUDA设备函数采用的Itanium C++ ABI修饰名（CUDA设备代码基于LLVM编译，遵循该跨平台ABI标准）。
• Dependency Walker中看到的??Kustruct@@QEBA?AV0@H@Z是MSVC对C++主机函数采用的Microsoft专用修饰名，属于完全独立的命名规则体系。

关键疑问解答 #

1. Dependency Walker是否修改了导出名称？ #

没有。它只是读取DLL导出表中的原始符号并按自身规则解析：

• 你看到的Microsoft风格修饰名是库中主机端导出函数的符号，而CUDA设备函数不会出现在DLL的导出表中——设备函数是运行在GPU上的代码，无法通过常规DLL导出机制对外暴露。
• 现代版本Dependencies工具显示未修饰名，是因为它自动解析了MSVC的修饰名，但对NVCC生成的Itanium风格修饰名无法识别，所以不会显示（或设备函数根本没被导出）。

2. NVCC是否采用了双修饰规则？ #

是的，但分场景：

• 设备函数：NVCC使用Itanium C++ ABI修饰规则（_ZN...格式），因为设备代码的编译后端基于LLVM，遵循跨平台标准。
• 主机函数：NVCC会调用MSVC编译器处理主机代码，所以主机函数使用MSVC的专用修饰规则（??...格式）。

解决步骤 #

1. 修正CUDA库的构建方式 #

• 不要将CUDA设备函数编译到动态库（DLL）中：设备代码无法被DLL导出，必须编译为静态库（.lib），这样调用项目才能链接到设备函数的二进制代码。
• 确保库中的设备函数正确声明：在库的头文件中用__device__ extern声明函数，例如：

  // 库头文件
  extern "C" {
      __device__ void ustructa(const ustruct&);
  }
  

  （若使用C++命名空间，需保证调用端命名空间一致，或用extern "C"规避名称修饰差异）
• 编译库时，确保NVCC启用设备代码生成：在VS项目设置中，进入配置属性 → CUDA C/C++ → 设备 → 代码生成，选择对应GPU架构（如compute_75,sm_75）。

2. 统一调用项目的编译设置 #

• 调用项目与库项目使用相同的CUDA版本、MSVC版本，避免ABI不兼容。
• 调用项目的.cu文件中，必须包含库的头文件，且函数声明与库中的定义完全一致（包括__device__修饰符、参数类型、命名空间）。
• 链接时，确保将静态库的路径和.lib文件添加到项目的链接器输入中。

3. 验证设备函数的存在 #

• 用dumpbin /SYMBOLS工具查看库的.lib文件，搜索Itanium风格的修饰名（如_ZN7ustructaSERKS_），确认设备函数的符号存在。若不存在，说明库的编译过程中未正确生成设备代码。

内容的提问来源于stack exchange，提问作者Rich Tanenbaum