1

我有一个包含许多源文件的项目（例如：main.cu、a.cu、b.cu、c.cu、d.cu）。每个都有函数和内核调用（全局和设备）。

在标头 (cpu.h) 中，所有要在主机端使用的结构和定义。另一个头文件（gpu.h）是设备端要使用的所有结构和定义。

  1. 如果我从main.cu调用内核函数，在a.cu中声明。如何#include在a.cu中声明以在main.cu中使用的那些内核函数，而不执行不推荐的#include "a.cu"？

  2. 我是否在a.cu中创建带有内核函数前向声明的标头啊？示例： extern void functionA(type);

那么 CUDA 内核函数呢？我应该为从另一个源文件中使用的每个源文件创建一个头文件吗？

  • 在哪里可以找到一些包含多个源文件的简单 CUDA 示例？

我提到 Nsight Eclipse 是因为我在使用它和多个来源时遇到了很多麻烦。我在 Ubuntu Linux 和 Mac OS 环境中使用 CUDA 5.5 Toolkits。我的主要开发环境是在 Ubuntu Linux 机器上使用 4 个 Tesla C1060 卡。

4

1 回答 1

3

  1. 分离内核。在一个项目中，创建两个文件（我重构了默认的 Runtime Project 模板并创建了 device.cu 和 host.cu）

    设备.cu：

    __device__ unsigned int bitreverse(unsigned int number) {
    number = ((0xf0f0f0f0 & number) >> 4) | ((0x0f0f0f0f & number) << 4);
    number = ((0xcccccccc & number) >> 2) | ((0x33333333 & number) << 2);
    number = ((0xaaaaaaaa & number) >> 1) | ((0x55555555 & number) << 1);
    return number;
}

__global__ void bitreverse(void *data) {
    unsigned int *idata = (unsigned int*) data;
    idata[threadIdx.x] = bitreverse(idata[threadIdx.x]);
}

    主机.cu：

    extern __global__ void bitreverse(void *data);

...

bitreverse<<<1, WORK_SIZE, WORK_SIZE * sizeof(int)>>>(d);

  2. 单独编译

    1. 右键单击项目，转到属性。
    2. 构建/设置。
    3. 为 SM 2.0 或更高版本设置构建。
    4. 选择“单独编译”单选。

    设备.cu：

    __device__ unsigned int bitreverse(unsigned int number) {
    number = ((0xf0f0f0f0 & number) >> 4) | ((0x0f0f0f0f & number) << 4);
    number = ((0xcccccccc & number) >> 2) | ((0x33333333 & number) << 2);
    number = ((0xaaaaaaaa & number) >> 1) | ((0x55555555 & number) << 1);
    return number;
}

    主机.cu：

    extern __device__ unsigned int bitreverse(unsigned int number);

__global__ void bitreverse(void *data) {
    unsigned int *idata = (unsigned int*) data;
    idata[threadIdx.x] = bitreverse(idata[threadIdx.x]);
}

...

bitreverse<<<1, WORK_SIZE, WORK_SIZE * sizeof(int)>>>(d);

  3. 隔离 CUDA 代码一种常见的模式是将 CUDA 代码隔离在 .cu 文件中，这些文件具有封装内核调用的宿主函数。通过这种方式，您可以将此类 .cu 文件生成的目标文件链接到以 .cpp 或 .c 文件编写的主机代码。请记住，导出的主机代码功能应符合extern "C".c 文件可用。

extern声明可以放在 .h 文件中。请注意，具有 CUDA C 语法（__global__特定于 CUDA C）的 .h 文件不能包含在 .cpp 或 .c 中。

将文件添加到项目

通常我只是将文件复制到项目文件夹，右键单击项目并执行“刷新”。Nsight 将索引它们并包含在构建中。

从构建中排除文件

如果您绝对需要，您可以将设备代码复制到标头并包含标头（惯例是此类头文件具有 .cuh 扩展名，尽管 .h 的工作方式相同）。您可以包含 .cu - 问题是 Nsight 将此类文件视为源文件并尝试编译它们。您可以通过选中构建属性中构建子树中任何属性页面顶部的“从构建中排除资源”复选框来从构建中排除 .cu 文件。

CUDA 多文件示例

几乎所有重要的样本都被分解成多个文件。只需从例如“粒子”示例创建一个 Nsight 项目。

于 2013-09-30T20:12:30.320 回答