Jak mogę pobrać informacje o liście parametrów dla jądra CUDA 4.0+?

Question

Zgodnie z dokumentacją NVidia dla cuLaunchKernel function, kernele skompilowane z CUDA 3.2+ zawierają informacje dotyczące ich listy parametrów. Czy istnieje sposób na pobieranie tych informacji programowo z uchwytu CUfunction? Muszę znać liczbę argumentów i rozmiar każdego argumentu w bajtach jądra z jego uchwytu CUfunction. Widziałem wyżej wspomnianą dokumentację NVidii mówiącą, że te informacje istnieją, ale nie widziałem nigdzie w dokumentacji CUDA wskazującej na programowy sposób dostępu do tych informacji.

Aby dodać trochę więcej wyjaśnień: Pracuję z systemem middleware. Jego frontside biblioteka zastępuje libcuda (biblioteka API sterownika) w systemie docelowym. Tylna strona działa wtedy jako demon na innym hoście, który używa zasób GPGPU i wywołuje prawdziwą libcudę na tym komputerze. Istnieją inne rozwiązania middleware, które już to robią w cuLaunchKernel, więc jest to zdecydowanie możliwe. Również sama CUDA używa tych informacji, aby wiedzieć, jak analizować parametry od wskaźnika, który przekazujesz do cuLaunchKernel.

Edytuj: Pierwotnie miałem wersję CUDA, w której wprowadzone metadane zostały nieprawidłowo podane. To było 3,2, nie 4,0, zgodnie z cuLaunchKernel documentation.

Answer 1

cuLaunchKernel jest przeznaczony do uruchamiania jąder, dla których znasz prototyp funkcji. Nie ma API dla "reverse engineering" prototypu funkcji.

Answer 2

Pracuję nad tym samym problemem (nie wiem, czy w międzyczasie rozwiązałeś go). Używam znanego jądra, aby zbadać, w jaki sposób używana jest che śpiczasta pamięć. To jest wersja żadne parametry:

#include<cstdio> 

extern "C" { 
    __global__ void HelloWorld(){ 
     int thid = (blockIdx.x * blockDim.x) + threadIdx.x; 
    } 
} 

To jest wersja jednego parametru i tak dalej.

#include<cstdio> 

extern "C" { 
    __global__ void HelloWorld(int a) { 
     int thid = (blockIdx.x * blockDim.x) + threadIdx.x; 
    } 
} 

Proponuję zrzucić pierwsze 1024 bajty pamięci wskazanej przez CUfunction i postępować zgodnie ze wskazówkami. Na przykład przy przesunięciu 0x30 znajduje się wskaźnik wskazujący na tabelę wskaźników. Zauważyłem, że rozmiar struktury opublikowanej przez CUfunction nie zmienia się wraz z liczbą parametrów funkcji, więc tabela, której szukamy, musi zostać polowana zgodnie ze wskazówkami.