CUDA `__device_builtin__` 宏解析：編譯器內部標記，對開發者透明

結論

__device_builtin__ 是 **CUDA 編譯器內部使用的空宏定義**，對開發者**無任何語義影響**，完全可以忽略。

代碼證據

// driver_types.h 中
#define __device_builtin__

// 枚舉定義
enum __device_builtin__ cudaError { ... };

// typedef 使用
typedef __device_builtin__ enum cudaError cudaError_t;

展開後等價於

enum cudaError { ... };
typedef enum cudaError cudaError_t;

為什麼要有這個宏？

• 編譯器標記：幫助 NVCC 編譯器識別「內建設備端類型/函數」，區分用戶自定義類型。
• 代碼生成控制：在內部編譯流程中決定是否生成設備端符號表、調試信息等。
• 版本兼容：作為保留關鍵字位置，未來擴展語義時不破壞現有代碼語法。

類比：MFC 的 AFX_MSG

// afxwin.h
#define AFX_MSG

// 用戶代碼
class CMyWnd : public CWnd {
    AFX_MSG void OnPaint();  // 展開後 void OnPaint();
};

同樣是**給框架工具（Class Wizard）識別用的標記**，預處理後消失，不影響 C++ 語義。

開發者應對

1. 直接忽略：閱讀 CUDA 頭文件時，心理自動過濾 __device_builtin__。
2. 不要在自定義代碼中使用：雙下劃線開頭屬於實現保留標識符，用戶代碼使用屬未定義行為。
3. 關注實質：cudaError_t 本質是 enum cudaError 的別名，錯誤碼值定義在枚舉中（如 cudaSuccess=0）。

延伸：CUDA 常見內部宏

宏	用途	開發者可見性
__host__	函數僅在宿主編譯	高（常用）
__device__	函數僅在設備編譯	高（常用）
__global__	Kernel 函數入口	高（核心）
__forceinline__	強制內聯	中（優化）
__device_builtin__	內建類型標記	無（忽略）
__builtin__	編譯器內建函數	低（間接使用）

看懂頭文件不等於要用內部宏，專注於公開 API（__global__、__device__、錯誤碼枚舉值），才是高效 CUDA 開發的正道。