警告：不允许从 __host__ __device__ 函数调用 __host__ 函数

Question

我参考了几乎所有类似的问题，但没有找到答案。错误检查被很多人推荐，所以我尝试使用CHECKED_CALL()类型的宏来使程序强大，但是我的代码遇到了两个问题：

1. 正如标题所说，我收到了一条警告消息，但在我使用#pragma hd_warning_disable之前，我收到了错误消息：

   cuEntityIDBuffer.cu(9): error: identifier "stderr" is undefined in device code

2. 当我编译maintest.cpp时，我得到另一个错误：

编辑：

 g++ -c maintest.cpp -std=c++11
 cuEntityIDBuffer.h:1:27: fatal error: thrust/reduce.h: No such file or directory

但是，在编译cuEntityIDBuffer.cu时它工作正常cuEntityIDBuffer.h也包含在这个文件中。
nvcc -arch=sm_35 -Xcompiler '-fPIC' -dc cuEntityIDBuffer.cu

cuEntityIDBuffer.cu 和 maintest.cpp #include "cuEntityIDBuffer.h"，但 maintest.cpp 抛出错误，我对此没有任何想法。

代码如下：

cuEntityIDBuffer.h

#include <thrust/reduce.h>
#include <thrust/execution_policy.h>
#include <stdio.h>
#include <assert.h>
#include <cuda_runtime.h>

#ifdef __CUDACC__
#define CUDA_CALLABLE_MEMBER __host__ __device__
#else
#define CUDA_CALLABLE_MEMBER
#endif

class cuEntityIDBuffer
{
public:
    CUDA_CALLABLE_MEMBER cuEntityIDBuffer();
    CUDA_CALLABLE_MEMBER cuEntityIDBuffer(unsigned int* buffer);
    CUDA_CALLABLE_MEMBER void cuCallBackEntityIDBuffer(unsigned int* buffer);
    CUDA_CALLABLE_MEMBER ~cuEntityIDBuffer();
    CUDA_CALLABLE_MEMBER void cuTest();
private:
    size_t buffersize;
    unsigned int* cuBuffer;
};

cuEntityIDBuffer.cu

#include "cuEntityIDBuffer.h"
#include <stdio.h>
#pragma hd_warning_disable
#define nTPB 256
#define gpuErrchk(ans) { gpuAssert((ans), __FILE__, __LINE__); }
inline void gpuAssert(cudaError_t code, const char *file, int line, bool abort=true)
{
   if (code != cudaSuccess) 
   {
      fprintf(stderr,"GPUassert: %s %s %d\n", cudaGetErrorString(code), file, line);
      if (abort) exit(code);
   }
}

__global__ void mykernel(unsigned int* buffer)
{
    int idx = threadIdx.x + (blockDim.x * blockIdx.x);
    buffer[idx]++;
    //other things.
}

cuEntityIDBuffer::cuEntityIDBuffer()
{
    buffersize=1024;
    gpuErrchk(cudaMalloc(&cuBuffer, buffersize * sizeof(unsigned int)));
}

cuEntityIDBuffer::cuEntityIDBuffer(unsigned int* buffer)
{
    buffersize=1024;
    gpuErrchk(cudaMalloc(&cuBuffer, buffersize * sizeof(unsigned int)));
    gpuErrchk(cudaMemcpy(cuBuffer,buffer,buffersize*sizeof(unsigned int),cudaMemcpyHostToDevice));
}

void cuEntityIDBuffer::cuCallBackEntityIDBuffer(unsigned int* buffer)
{
    gpuErrchk(cudaMemcpy(buffer,cuBuffer,buffersize*sizeof(unsigned int),cudaMemcpyDeviceToHost));
}

cuEntityIDBuffer::~cuEntityIDBuffer()
{
    gpuErrchk(cudaFree((cuBuffer)));
}

void cuEntityIDBuffer::cuTest()
{
    mykernel<<<((buffersize+nTPB-1)/nTPB),nTPB>>>(cuBuffer);
    gpuErrchk(cudaPeekAtLastError());
}

maintest.cpp

#include "cuEntityIDBuffer.h"
#include <iostream>

int main(int argc, char const *argv[])
{
    unsigned int *h_buf;
    h_buf=malloc(1024*sizeof(unsigned int));
    cuEntityIDBuffer d_buf(h_buf);
    d_buf.cuTest();
    d_buf.cuCallBackEntityIDBuffer(h_buf);
    return 0;
}

是我使用CHECKED_CALL() 类型宏的方式错误还是我的代码组织有问题？任何建议表示赞赏。

Answer 1

您的方法定义为__host__ 和__device，这意味着它们将为CPU 编译一次，为设备编译一次。我认为 CPU 版本没有什么大问题。但是，您的设备版本有两个问题：

• cuEntityIDBuffer.cu(9): error: identifier "stderr" is undefined in device code 很清楚，你尝试在设备代码中使用 CPU 变量stderr。

• warning: calling a __host__ function from a __host__ __device__ function is not allowed 是同一种问题：没有任何__host__、__device__ 或__global__ 属性，符号被隐式设置为__host__，这意味着在您的情况下设备版本您的一些方法正在尝试使用仅在 CPU 端的gpuAssert。

对于cuEntityIDBuffer.h:1:27: fatal error: thrust/reduce.h: No such file or directory，正如@Talonmies 指出的那样，任何推力代码都必须使用nvcc 构建。