在 Cuda 内核中使用 c++ 对象和类成员

Posted

技术标签:

【中文标题】在 Cuda 内核中使用 c++ 对象和类成员【英文标题】:Using c++ objects and class members inside a Cuda kernel 【发布时间】:2021-12-26 15:15:42 【问题描述】:

我是 C++ 新手,尤其是 Cuda 计算工具。我正在尝试使用 Cuda 在 GPU 上并行化我的代码,出于我的目的,有必要能够从一个类中创建对象,或者至少能够从内核中调用它们的成员。

首先是我的类的定义:

//Header
#pragma once
#include<cuda.h>
#include<cuda_runtime.h>
#include<cuda_runtime_api.h>
#include<stdio.h>
#include<iostream>

class Ding

private:
    int index;
    double vector_1[100];
    double vector_2[100];
    double prop;

public:
    __host__ __device__ Ding(int);
    __host__ __device__ ~Ding();

    __device__ void calculate_stuff(double, int);
    __device__ double get_prop();
;

//Source
#include "Ding.h"
#include <math.h>

__host__ __device__ Ding::Ding(int ind) 
    index = ind;
    prop = 1;
    for (int ii = 0; ii < 100; ii++) 
        vector_1[ii] = (4 * ii + ind) / (ind + ii + 1);
        vector_2[ii] = (-2.14 * ii + ind) / (2*ind + ii + 1);
    


__host__ __device__ Ding::~Ding() ;

__device__ void Ding::calculate_stuff(double coeff, int N) 
    prop = 1;

    for (int ii = 0; ii < N; ii++) 
        for (int jj = 0; jj < 100; jj++) 
            prop += pow(-1, ii) * vector_1[jj] * vector_2[jj]*coeff;
        
    


__device__ double Ding::get_prop() 
    return prop;

正如您所看到的,除了执行了一些无意义的计算之外,这没什么大不了的,因为这只能作为我如何使用 Cuda 运行此代码的示例。

现在这里是主要的源文件:

#include<cuda.h>
#include<cuda_runtime.h>
#include<cuda_runtime_api.h>
#include "device_launch_parameters.h"
#include<stdio.h>
#include<iostream>
#include "Ding.h"

using namespace std;

__global__ void some_kernel(double *vec_a, Ding* teil, int size) 
    int ii = blockIdx.x * blockDim.x + threadIdx.x;

    if (ii < size) 
        vec_a[ii] += teil[ii].get_prop();
        vec_a[ii] += ii;
    


int main() 
    double* vec_1, * d_vec_1;
    int N = 300;
    double result = 0;
    Ding* teil;
    Ding* d_teil;

    vec_1 = (double*)malloc(N * sizeof(double));
    teil = (Ding*)malloc(N * sizeof(Ding));
    for (int ii = 0; ii < N; ii++) 
        vec_1[ii] = 0;
        teil[ii] = Ding::Ding(ii);
    

    cudaMalloc(&d_vec_1, N * sizeof(double));
    cudaMalloc(&d_teil, N * sizeof(Ding));

    cudaMemcpy(d_vec_1, vec_1, N * sizeof(double), cudaMemcpyHostToDevice);
    cudaMemcpy(d_teil, teil, N * sizeof(Ding), cudaMemcpyHostToDevice);


    some_kernel <<< 256/N + 1, 256 >>> (d_vec_1, d_teil,  N);

    for (int ii = 0; ii < N; ii++) 
        result += vec_1[ii];
    
    
    cout << "Old result: " << result << endl;

    cudaMemcpy(vec_1, d_vec_1, N * sizeof(double), cudaMemcpyDeviceToHost);
    
    result = 0;

    for (int ii = 0; ii < N; ii++) 
        result += vec_1[ii];
    

    cout << "New result: " << result << endl;

我从主机创建了一个对象数组并将其复制到设备。在设备上,仅调用参数“prop”的 getter,并将该值添加到向量 vec_a。所以基本上,当没有从设备调用类成员时,代码就可以工作。所以如果我注释掉这一行:

vec_a[ii] += teil[ii].get_prop();

代码有效,但一旦任何班级成员开始发挥作用,我就会收到以下错误,不幸的是我无法理解:

Fehler MSB3721 Der Befehl ""C:\Program Files\NVIDIA GPU Computing Toolkit\CUDA\v11.4\bin\nvcc.exe" -gencode=arch=compute_52,code=sm_52 --use-local-env - ccbin "C:\Program Files (x86)\Microsoft Visual Studio\2019\Community\VC\Tools\MSVC\14.29.30133\bin\HostX86\x64" -x cu -I"C:\Program Files\NVIDIA GPU Computing Toolkit\CUDA\v11.4\include" -I"C:\Program Files\NVIDIA GPU Computing Toolkit\CUDA\v11.4\include" -G --keep-dir x64\Debug -maxrregcount=0 --machine 64 -cuda -cudart static -g -D_DEBUG -D_CONSOLE -D_UNICODE -DUNICODE -Xcompiler "/EHsc /W3 /nologo /Od /Fdx64\Debug\vc142.pdb /FS /Zi /RTC1 /MDd " -o x64\Debug\File .cu.obj "C:\Users\ronal\source\repos\Basic_Cuda_Test\Basic_Cuda_Test\File.cu"" wurde mit Code 255 bedet。 Basic_Cuda_Test C:\Program Files (x86)\Microsoft Visual Studio\2019\Community\MSBuild\Microsoft\VC\v160\BuildCustomizations\CUDA 11.4.targets 785

从这条消息中可以看出,我使用的是 Cuda v11.4 和 Microsoft Visual Studio 2019。在不访问类成员的情况下,计算成功执行,因此 Cuda 的东西似乎可以正常工作。这就是为什么我假设到目前为止一切都已正确安装和配置。如果我也可以在设备上创建对象最好,但现在如果我能以某种方式利用设备上的类成员,我会非常高兴。可能问题很基本。

我期待您的回答和解决方案。

【问题讨论】:

【参考方案1】:

从给出的代码来看,我假设您有一些文件Ding.cu,其中包含Ding 的实现。 为了能够从不同的翻译单元(内核在main.cu 中实现)调用设备函数,必须生成可重定位的设备代码。使用编译器标志--rdc=true

【讨论】:

以上是关于在 Cuda 内核中使用 c++ 对象和类成员的主要内容,如果未能解决你的问题,请参考以下文章

在 CUDA 中选择性地编译头文件和类函数

访问不同 CUDA 内核中的类成员

为什么CUDA会在访问课程成员时崩溃?

C++ 类和对象

C++ 类和对象

C++ 类和对象