12

我正在使用 CUDA,并且我创建了一个int2_类来处理复整数。

文件中的类声明ComplexTypes.h如下:

namespace LibraryNameSpace
{
    class int2_ {

        public:
            int x;
            int y;

            // Constructors
            __host__ __device__ int2_(const int,const int);
            __host__ __device__ int2_();
            // etc.

            // Equalities with other types      
            __host__ __device__ const int2_& operator=(const int);
            __host__ __device__ const int2_& operator=(const float);
            // etc.

    };
}

文件中的类实现ComplexTypes.cpp如下:

#include "ComplexTypes.h"

__host__ __device__         LibraryNameSpace::int2_::int2_(const int x_,const int y_)           { x=x_; y=y_;}
__host__ __device__         LibraryNameSpace::int2_::int2_() {}
// etc.

__host__ __device__ const   LibraryNameSpace::int2_& LibraryNameSpace::int2_::operator=(const int a)                        { x = a;            y = 0.;             return *this; }
__host__ __device__ const   LibraryNameSpace::int2_& LibraryNameSpace::int2_::operator=(const float a)                      { x = (int)a;       y = 0.;             return *this; }
// etc.

一切正常。在main(包括ComplexTypes.h)中,我可以处理int2_数字。

CudaMatrix.cu文件中,我现在包含ComplexTypes.h并定义并正确实例化该__global__函数:

template <class T1, class T2>
__global__ void evaluation_matrix(T1* data_, T2* ob, int NumElements)
{
    const int i = blockDim.x * blockIdx.x + threadIdx.x;
    if(i < NumElements) data_[i] = ob[i];
}

template __global__ void evaluation_matrix(LibraryNameSpace::int2_*,int*,int);

文件的情况CudaMatrix.cu似乎与main函数对称。然而,编译器抱怨:

Error   19  error : Unresolved extern function '_ZN16LibraryNameSpace5int2_aSEi'    C:\Users\Documents\Project\Test\Testing_Files\ptxas simpleTest

请考虑:

  1. 在将实现移动到单独的文件之前,当在文件中包含声明和实现时,一切都正常工作main
  2. 有问题的指令是data_[i] = ob[i].

任何人都知道发生了什么?

4

1 回答 1

23

我在上面的帖子中遵循的程序有两个问题:

  1. 必须ComplexTypes.cpp文件名转换为可以拦截 CUDA 关键字和. Talonmies 在他的评论中指出了这一点。实际上,在发布之前,我已经将文件名从 更改为,但编译器抱怨并显示相同的错误。所以,我才天真地退后一步;ComplexTypes.cunvcc__device____host__.cpp.cu

  2. 在 Visual Studio 2010 中,必须使用View -> Property Pages;配置属性 -> CUDA C/C++ -> 通用 -> 生成可重定位设备代码 -> 是 (-rdc=true)。这是单独编译所必需的。事实上,在NVIDIA CUDA Compiler Driver NVCC,据说:

CUDA 通过将设备代码嵌入到主机对象中来工作。在整个程序编译中,它将可执行设备代码嵌入到宿主对象中。在单独编译中,我们将可重定位设备代码嵌入到宿主对象中,并运行设备链接器(nvlink)将所有设备代码链接在一起。然后通过主机链接器将 nvlink 的输出与所有主机对象链接在一起,形成最终的可执行文件。可重定位与可执行设备代码的生成由--relocatable-device-code={true,false}选项控制,该选项可以缩写为–rdc={true,false}

于 2013-06-19T12:15:44.127 回答