CUDA与MSVC编译错误：<atomic>头文件标识符未定义

环境信息 #

• 主机编译器：Visual Studio 2019 MSVC v14.29.30133
• CUDA版本：12.3
• 构建工具：mingw32-make

编译命令 #

$ mingw32-make -f Makefile
D:/za/mingw/mingw64/bin/mingw32-make -f Makefile.Release
mingw32-make[1]: Entering directory 'D:/za/conformal_flow/flo/flo'
"C:\Program Files\NVIDIA GPU Computing Toolkit\CUDA\v12.3/bin/nvcc" -ccbin "C:/Program Files (x86)/Microsoft Visual Studio/2019/Community/VC/Tools/MSVC/14.29.30133/bin/Hostx64/x64/cl" -arch=sm_61 -Xptxas -O3 --use_fast_math --restrict --expt-relaxed-constexpr --expt-extended-lambda -DUNICODE -D_UNICODE -DWIN32 -DMINGW_HAS_SECURE_API=1 -DTHRUST_DEVICE_SYSTEM=THRUST_DEVICE_SYSTEM_CUDA  -Xcudafe --display_error_number -Xcudafe --diag_suppress=2906 -Xcudafe --diag_suppress=186  -ID:/za/conformal_flow/flo/dep/eigen -ID:/za/conformal_flow/flo/dep/libigl/include -ID:/za/conformal_flow/flo/flo/include -I"D:/za/conformal_flow/flo/dep/cusplibrary" -I"C:\Program Files\NVIDIA GPU Computing Toolkit\CUDA\v12.3/include" -I"C:\Program Files\NVIDIA GPU Computing Toolkit\CUDA\v12.3/include/cuda"  src/flo/device/adjacency_matrix_indices.cu -o cudaobj/adjacency_matrix_indices.o -L"C:\Program Files\NVIDIA GPU Computing Toolkit\CUDA\v12.3/lib/x64" -lcudart -lcurand -licudata -lcudart_static -lcudadevrt -lcusparse -lcusolver -dc

错误信息 #

C:\Program Files\NVIDIA GPU Computing Toolkit\CUDA\v12.3\include\cuda\std\detail\libcxx\include\__cuda/atomic_prelude.h(21): error: identifier "ATOMIC_XXX_LOCK_FREE" is undefined
      static_assert(ATOMIC_XXX_LOCK_FREE == 2, "");
                    ^
C:/Program Files/NVIDIA GPU Computing Toolkit/CUDA/v12.3/include\cub/util_device.cuh(237): error: namespace "std" has no member "atomic"
          std::atomic<DeviceEntryStatus> flag;
               ^
C:/Program Files/NVIDIA GPU Computing Toolkit/CUDA/v12.3/include\cub/util_device.cuh(237): error: this declaration has no storage class or type specifier
          std::atomic<DeviceEntryStatus> flag;
          ^

C:/Program Files/NVIDIA GPU Computing Toolkit/CUDA/v12.3/include\cub/util_device.cuh(237): error: expected a ";"
          std::atomic<DeviceEntryStatus> flag;
                     ^

C:/Program Files/NVIDIA GPU Computing Toolkit/CUDA/v12.3/include\cub/util_device.cuh(266): error: class "cub::CUB_200200_610_NS::PerDeviceAttributeCache::DeviceEntry" has no member "flag"
          auto& flag    = entry.flag;
                                ^

注：XXX代表BOOL、CHAR、CHAR16_T等基础类型

已排查情况 #

• 确认atomic_prelude.h中包含<atomic>头文件，且该头文件存在于MSVC的标准包含路径C:\Program Files (x86)\Microsoft Visual Studio\2019\Community\VC\Tools\MSVC\14.29.30133\include中
• 尝试添加编译选项-Xcompiler -std=c++11，问题未解决

原因分析 #

1. 版本兼容性不匹配：CUDA 12.3要求主机编译器至少为MSVC 2019 Update 16.11（对应v14.29.30137及以上），当前使用的v14.29.30133是Update 10版本，过低的版本无法支持CUDA 12.3依赖的<atomic>完整特性。
2. nvcc预处理逻辑问题：nvcc处理CUDA标准库头文件时，旧版MSVC的<atomic>未实现ATOMIC_XXX_LOCK_FREE宏和std::atomic的完整定义，导致预处理阶段符号无法识别。
3. 编译选项传递错误：仅通过-Xcompiler给主机编译器传-std=c++11没用，nvcc需要直接指定-std选项来控制整个编译流程的C++标准版本。

解决方案 #

方案1：升级MSVC到兼容版本 #

安装Visual Studio 2019 Update 16.11或更高版本，确保MSVC版本达到v14.29.30137及以上，之后让nvcc指向更新后的编译器路径重新编译。

方案2：调整CUDA编译选项 #

1. 添加nvcc的C++标准指定：在编译命令中加入-std=c++14（或更高版本如-std=c++17），替换仅通过-Xcompiler传递的选项，示例修改后的编译片段：

   "C:\Program Files\NVIDIA GPU Computing Toolkit\CUDA\v12.3/bin/nvcc" -ccbin ".../cl" -std=c++14 -arch=sm_61 ...
   

2. 移除冲突宏定义：-DMINGW_HAS_SECURE_API=1是mingw相关的宏，可能干扰MSVC标准库处理，尝试删除该宏后重新编译。

方案3：降级CUDA版本 #

如果无法升级MSVC，可将CUDA降级到11.x系列（如CUDA 11.7），该版本对MSVC 2019 Update 10兼容性更好，同时确认项目依赖的CUDA特性在降级版本中可用。

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