OpenCL 設備資訊查詢完整指南：clGetDeviceInfo 深度解析

為什麼要查詢設備資訊？

GPGPU 程式優化的前提是「知己知彼」。不同 GPU 的計算單元 (CU) 數量、處理元素 (PE) 數量、本地記憶體大小、最大工作群組尺寸等參數差異極大。盲目編寫 Kernel 而不針對硬體特性調優，效能往往差強人意。clGetDeviceInfo 正是獲取這些關鍵參數的標準介面。

API 原型與雙階段調用機制

cl_int clGetDeviceInfo(
    cl_device_id device,           // 目標設備 ID
    cl_device_info param_name,     // 查詢參數枚舉
    size_t param_value_size,       // 緩衝區大小
    void* param_value,             // 緩衝區指標
    size_t* param_value_size_ret   // 實際返回大小
);

核心機制：必須調用兩次：

1. 第一次：param_value = NULL，param_value_size = 0，獲取 param_value_size_ret 確定所需緩衝區大小
2. 第二次：分配足夠緩衝區，再次調用獲取實際資料

常用查詢參數速查表

完整程式碼範例

#include <CL/cl.h>
#include <stdio.h>
#include <stdlib.h>
#include <string.h>

void print_device_info(cl_device_id device) {
    cl_int err;
    size_t size;
    
    // 1. 獲取設備名稱
    err = clGetDeviceInfo(device, CL_DEVICE_NAME, 0, NULL, &size);
    char* name = (char*)malloc(size);
    clGetDeviceInfo(device, CL_DEVICE_NAME, size, name, NULL);
    printf("Device: %s\n", name);
    free(name);
    
    // 2. 獲取計算單元數量
    cl_uint cu_count;
    clGetDeviceInfo(device, CL_DEVICE_MAX_COMPUTE_UNITS, 
                    sizeof(cl_uint), &cu_count, NULL);
    printf("Compute Units: %u\n", cu_count);
    
    // 3. 獲取本地記憶體大小
    cl_ulong local_mem;
    clGetDeviceInfo(device, CL_DEVICE_LOCAL_MEM_SIZE,
                    sizeof(cl_ulong), &local_mem, NULL);
    printf("Local Memory: %llu KB\n", local_mem / 1024);
    
    // 4. 獲取最大工作群組尺寸
    size_t max_wg_size;
    clGetDeviceInfo(device, CL_DEVICE_MAX_WORK_GROUP_SIZE,
                    sizeof(size_t), &max_wg_size, NULL);
    printf("Max Work Group Size: %zu\n", max_wg_size);
    
    // 5. 獲取支援的擴展
    err = clGetDeviceInfo(device, CL_DEVICE_EXTENSIONS, 0, NULL, &size);
    char* exts = (char*)malloc(size);
    clGetDeviceInfo(device, CL_DEVICE_EXTENSIONS, size, exts, NULL);
    printf("Extensions: %s\n", exts);
    free(exts);
}

int main() {
    cl_platform_id platform;
    clGetPlatformIDs(1, &platform, NULL);
    
    cl_device_id device;
    clGetDeviceIDs(platform, CL_DEVICE_TYPE_GPU, 1, &device, NULL);
    
    print_device_info(device);
    return 0;
}

實戰應用：動態調整 Kernel 參數

// 根據查詢結果動態設定 local work size
size_t local_size;
clGetDeviceInfo(device, CL_DEVICE_MAX_WORK_GROUP_SIZE, 
                sizeof(size_t), &local_size, NULL);

// 確保不超過硬體限制，並嘗試 2 的冪次方以獲得最佳效能
size_t optimal_local = 1;
while (optimal_local * 2 <= local_size && optimal_local * 2 <= 256) {
    optimal_local *= 2;
}

// 啟動 Kernel
size_t global_size = (data_size + optimal_local - 1) / optimal_local * optimal_local;
clEnqueueNDRangeKernel(queue, kernel, 1, NULL, &global_size, &optimal_local, 0, NULL, NULL);

常見錯誤與避坑

• 忘記檢查返回碼：CL_INVALID_DEVICE、CL_INVALID_VALUE 都會導致查詢失敗
• 緩衝區太小：第一次查詢大小是必要步驟，不要硬編碼緩衝區大小
• 忽略擴展支援：使用 cl_khr_fp16、cl_khr_int64_base_atomics 等擴展前必須先查詢確認