引言:本人初学cuda编程,在jetson nano 4G上想实现sliced wasserstein distance的各个slice并行加速计算,遇到一些问题和解决方案,记录在此。
基础知识:在cuda编程中,cpu称作host,gpu称作device。在gpu上并行运算的函数称作kernel function,其编写在.cu, .cuh程序中,与.cpp, .h对应。编译规则可以用同目录下的对应的CMakeList.txt。
问题:编译报错如下
error: calling a constexpr __host__ function("make_pair") from a __global__ function("emd") is not allowed. The experimental flag '--expt-relaxed-constexpr' can be used to allow this.
对应代码为kernel.cu的:
for (int i = 0; i < M; i++) {
cloud1Idx[i] = std::make_pair(proj.proj(cloud1[i]), i);
}
中使用了std::make_pair这个std库中的函数。
解决方法如报错中所说,添加编译选项“--expt-relaxed-constexpr”在同目录下的对应的CMakeList.txt中:
set(CUDA_NVCC_FLAGS --expt-relaxed-constexpr)
随后报错消失。
参考:
【1】cuda - How to invoke a constexpr function on both device and host? - Stack Overflow