设备代码中 CUDA 类静态成员的惯用语？

Question

所以，我有一个 C++14 库，我正在将其移植到 CUDA 9。我实际上（我认为）对 CUDA 有很好的了解，但自 CUDA 6 以来我还没有在其中做过任何直接的工作。

通常，我在代码中使用大量模板和小类。令我惊讶的是，static __device__在 CUDA 9 中仍然无法拥有类成员，但全局变量却可以。有没有一个好的习惯用法或解决方法？人们通常做什么？

编辑：我应该清楚，我的意思是专门针对模板类。如果该类没有模板化，那就非常简单了。

编辑2：这是一些示例代码

在普通的主机端 C++ 中，我这样做：

template <typename T>
class MyClass {
    static T my_static_member;
};

在设备上，这无法编译，那么什么是好的等效项呢？

template <typename T>
class MyClass {
    static __device__ T my_static_member;
};

Answer 1

您可以使用（模板化）全局变量而不是静态成员，并且可能将它们放在详细命名空间中：

namespace detail {
namespace MyClass {

template <typename T> __device__ T my_static_member;

} // namespace detail
} // namespace MyClass

template <typename T>
class MyClass {

    // ... you use detail::MyClass::my_static_member<T> in the code
};

...但这不需要传递--std=C++14到nvcc.

进一步的修改 - 基本上是风格问题 - 可以添加一个非技术静态但某种类型的吸气剂：

template <typename T>
class MyClass {
    const T& my_static_member() const {
        return detail::MyClass::my_static_member<T>;
    }
    // ... you use my_static_member() in the code
};