summaryrefslogtreecommitdiffstats
path: root/userspace/cuda/570.144/annotations
diff options
context:
space:
mode:
authorArthur Hanson Rasmusson <arthur@vgpu.io>2026-09-23 12:11:04 -0400
committerArthur Hanson Rasmusson <arthur@vgpu.io>2026-09-23 12:11:04 -0400
commitf874d709e5a45d63c8ee9ab6b0300195aa5d20a5 (patch)
tree2d07208f789e402686ac960e5ad7456b6fd21cfd /userspace/cuda/570.144/annotations
parentae18e08d02500579f084616874d8f2ae57f8281b (diff)
downloadopen-iov-f874d709e5a45d63c8ee9ab6b0300195aa5d20a5.tar.gz
open-iov-f874d709e5a45d63c8ee9ab6b0300195aa5d20a5.zip
userspace/cuda: add CUDA userspace driver analysis, tooling and name maps
Add the analysis of the NVIDIA CUDA userspace driver used by Open-IOV VMs: * docs/01-08: architecture (layers, object model, threads, sync, memory, channels, launch), build and execution model, the driver/kernel/GPU interface contract, virtualization approaches, the 570.144 decompilation map with the corrected libcuda crash path and the current engine-topology blocker, tooling, and a version-upgrade playbook. * tools/: version-agnostic toolchain - stdlib ELF/interface toolkit (exports, unwind-table function map, wrapper resolution, version delta, crash address decode), callgraph walker, corpus annotator, and Ghidra analysis/decompilation/name-map scripts with resumable parallel drivers. * 570.144/annotations/: our name map (exports + resolved wrappers + verified internals) and subsystem index, tracked so naming work accumulates. * READ-ME-FIRST.md: reading guide with the fast lookup recipes. The full decompiled corpus and annotated corpus stay untracked (vendor- derived, gitignored under the version run/ tree).
Diffstat (limited to 'userspace/cuda/570.144/annotations')
-rw-r--r--userspace/cuda/570.144/annotations/README.md35
-rw-r--r--userspace/cuda/570.144/annotations/names.tsv1304
-rw-r--r--userspace/cuda/570.144/annotations/subsystems.tsv37
3 files changed, 1376 insertions, 0 deletions
diff --git a/userspace/cuda/570.144/annotations/README.md b/userspace/cuda/570.144/annotations/README.md
new file mode 100644
index 0000000..868c503
--- /dev/null
+++ b/userspace/cuda/570.144/annotations/README.md
@@ -0,0 +1,35 @@
+# Open-IOV CUDA analysis annotations (tracked)
+
+These files are our own work product: names, roles and evidence for functions
+in the CUDA userspace driver. They are tracked in git so that analysis effort
+accumulates across driver versions.
+
+## Files
+
+| File | Format | Purpose |
+|---|---|---|
+| `names.tsv` | `file_vaddr<TAB>name<TAB>source` | symbol map to apply to a Ghidra project (or any address-keyed analysis). `source` is `export`, `wrapper`, `verified`, or `todo`. |
+| `subsystems.tsv` | `file_vaddr<TAB>name<TAB>subsystem<TAB>role<TAB>evidence` | human-readable subsystem index: which function belongs to which layer and what it does, with the evidence for the claim. |
+
+Addresses are **file virtual addresses** (`libcuda+0x...`). Apply the map with
+`tools/ghidra/ApplyNameMap.java`; see `docs/06-tooling.md`.
+
+## How names.tsv is generated
+
+1. **Exports** — exact, from `.dynsym` (`tools/cudatool.py exports`).
+2. **Wrappers** — the generated `cu*` stubs jump through an interposition slot
+ whose initial value is a relocation to the generated wrapper function.
+ `tools/cudatool.py wrappers` resolves all of them; they are named
+ `wrapper_<export>`.
+3. **Verified internals** — functions read and understood during the
+ decompilation effort. Each is added by hand with evidence recorded in
+ `subsystems.tsv` and the public docs.
+4. **Transfers** — when a new driver version is analysed, apply the previous
+ map, check how many names land (`ApplyNameMap.java --dry-run`), fix the
+ misses, and record the delta for the version.
+
+## Rules
+
+* Never guess silently. A name without evidence is worse than `FUN_...`; put
+ open questions in `subsystems.tsv` with `evidence=todo` instead.
+* Names must describe behaviour, not vendor internals we cannot justify.
diff --git a/userspace/cuda/570.144/annotations/names.tsv b/userspace/cuda/570.144/annotations/names.tsv
new file mode 100644
index 0000000..403bef3
--- /dev/null
+++ b/userspace/cuda/570.144/annotations/names.tsv
@@ -0,0 +1,1304 @@
+# Open-IOV CUDA 570.144 name map (our own work product; tracked).
+# Format: <file_vaddr>\t<name>\t<source>
+# Addresses are FILE virtual addresses (libcuda+0x...). Apply with
+# tools/ghidra/ApplyNameMap.java; see annotations/README.md.
+#
+# --- exports (exact, from .dynsym) ---
+0x001dc040 cuMemGetAttribute export
+0x001dc050 cuMemGetAttribute_v2 export
+0x002414b0 cudbgReportDriverApiError export
+0x002414c0 cudbgReportDriverInternalError export
+0x00249c70 cudbgGetAPI export
+0x00249e40 cudbgGetAPIVersion export
+0x0024b1f0 cudbgApiAttach export
+0x0024b2a0 cudbgApiDetach export
+0x0025bbd0 cudbgApiInit export
+0x0026e470 cuEGLApiInit export
+0x00310020 cuGetErrorString export
+0x00310040 cuGetErrorName export
+0x00310060 cuInit export
+0x00310080 cuDriverGetVersion export
+0x003100a0 cuDeviceGet export
+0x003100c0 cuDeviceGetCount export
+0x003100e0 cuDeviceGetName export
+0x00310100 cuDeviceGetUuid export
+0x00310120 cuDeviceGetUuid_v2 export
+0x00310140 cuDeviceGetLuid export
+0x00310160 cuDeviceTotalMem_v2 export
+0x00310180 cuDeviceGetTexture1DLinearMaxWidth export
+0x003101a0 cuDeviceGetAttribute export
+0x003101c0 cuDeviceGetNvSciSyncAttributes export
+0x003101e0 cuDeviceSetMemPool export
+0x00310200 cuDeviceGetMemPool export
+0x00310220 cuDeviceGetDefaultMemPool export
+0x00310240 cuDeviceGetExecAffinitySupport export
+0x00310260 cuFlushGPUDirectRDMAWrites export
+0x00310280 cuDeviceGetProperties export
+0x003102a0 cuDeviceComputeCapability export
+0x003102c0 cuDevicePrimaryCtxRetain export
+0x003102e0 cuDevicePrimaryCtxRelease_v2 export
+0x00310300 cuDevicePrimaryCtxSetFlags_v2 export
+0x00310320 cuDevicePrimaryCtxGetState export
+0x00310340 cuDevicePrimaryCtxReset_v2 export
+0x00310360 cuCtxCreate_v2 export
+0x00310380 cuCtxCreate_v3 export
+0x003103a0 cuCtxCreate_v4 export
+0x003103c0 cuCtxDestroy_v2 export
+0x003103e0 cuCtxPushCurrent_v2 export
+0x00310400 cuCtxPopCurrent_v2 export
+0x00310420 cuCtxSetCurrent export
+0x00310440 cuCtxGetCurrent export
+0x00310460 cuCtxGetDevice export
+0x00310480 cuCtxGetFlags export
+0x003104a0 cuCtxSetFlags export
+0x003104c0 cuCtxGetId export
+0x003104e0 cuCtxSynchronize export
+0x00310500 cuCtxSetLimit export
+0x00310520 cuCtxGetLimit export
+0x00310540 cuCtxGetCacheConfig export
+0x00310560 cuCtxSetCacheConfig export
+0x00310580 cuCtxGetApiVersion export
+0x003105a0 cuCtxGetStreamPriorityRange export
+0x003105c0 cuCtxResetPersistingL2Cache export
+0x003105e0 cuCtxGetExecAffinity export
+0x00310600 cuCtxRecordEvent export
+0x00310620 cuCtxWaitEvent export
+0x00310640 cuCtxAttach export
+0x00310660 cuCtxDetach export
+0x00310680 cuCtxGetSharedMemConfig export
+0x003106a0 cuCtxSetSharedMemConfig export
+0x003106c0 cuModuleLoad export
+0x003106e0 cuModuleLoadData export
+0x00310700 cuModuleLoadDataEx export
+0x00310720 cuModuleLoadFatBinary export
+0x00310740 cuModuleUnload export
+0x00310760 cuModuleGetLoadingMode export
+0x00310780 cuModuleGetFunction export
+0x003107a0 cuModuleGetFunctionCount export
+0x003107c0 cuModuleEnumerateFunctions export
+0x003107e0 cuModuleGetGlobal_v2 export
+0x00310800 cuLinkCreate_v2 export
+0x00310820 cuLinkAddData_v2 export
+0x00310840 cuLinkAddFile_v2 export
+0x00310860 cuLinkComplete export
+0x00310880 cuLinkDestroy export
+0x003108a0 cuModuleGetTexRef export
+0x003108c0 cuModuleGetSurfRef export
+0x003108e0 cuLibraryLoadData export
+0x00310900 cuLibraryLoadFromFile export
+0x00310920 cuLibraryUnload export
+0x00310940 cuLibraryGetKernel export
+0x00310960 cuLibraryGetKernelCount export
+0x00310980 cuLibraryEnumerateKernels export
+0x003109a0 cuLibraryGetModule export
+0x003109c0 cuKernelGetFunction export
+0x003109e0 cuKernelGetLibrary export
+0x00310a00 cuLibraryGetGlobal export
+0x00310a20 cuLibraryGetManaged export
+0x00310a40 cuLibraryGetUnifiedFunction export
+0x00310a60 cuKernelGetAttribute export
+0x00310a80 cuKernelSetAttribute export
+0x00310aa0 cuKernelSetCacheConfig export
+0x00310ac0 cuKernelGetName export
+0x00310ae0 cuKernelGetParamInfo export
+0x00310b00 cuMemGetInfo_v2 export
+0x00310b20 cuMemAlloc_v2 export
+0x00310b40 cuMemAllocPitch_v2 export
+0x00310b60 cuMemFree_v2 export
+0x00310b80 cuMemGetAddressRange_v2 export
+0x00310ba0 cuMemAllocHost_v2 export
+0x00310bc0 cuMemFreeHost export
+0x00310be0 cuMemHostAlloc export
+0x00330590 cuMemHostGetDevicePointer_v2 export
+0x003305b0 cuMemHostGetFlags export
+0x003305d0 cuMemAllocManaged export
+0x003305f0 cuDeviceRegisterAsyncNotification export
+0x00330610 cuDeviceUnregisterAsyncNotification export
+0x00330630 cuDeviceGetByPCIBusId export
+0x00330650 cuDeviceGetPCIBusId export
+0x00330670 cuIpcGetEventHandle export
+0x00330690 cuIpcOpenEventHandle export
+0x003306b0 cuIpcGetMemHandle export
+0x003306d0 cuIpcOpenMemHandle_v2 export
+0x003306f0 cuIpcCloseMemHandle export
+0x00330710 cuMemHostRegister_v2 export
+0x00330730 cuMemHostUnregister export
+0x00330750 cuMemcpy_ptds export
+0x00330770 cuMemcpyPeer_ptds export
+0x00330790 cuMemcpyHtoD_v2_ptds export
+0x003307b0 cuMemcpyDtoH_v2_ptds export
+0x003307d0 cuMemcpyDtoD_v2_ptds export
+0x003307f0 cuMemcpyDtoA_v2_ptds export
+0x00330810 cuMemcpyAtoD_v2_ptds export
+0x00330830 cuMemcpyHtoA_v2_ptds export
+0x00330850 cuMemcpyAtoH_v2_ptds export
+0x00330870 cuMemcpyAtoA_v2_ptds export
+0x00330890 cuMemcpy2D_v2_ptds export
+0x003308b0 cuMemcpy2DUnaligned_v2_ptds export
+0x003308d0 cuMemcpy3D_v2_ptds export
+0x003308f0 cuMemcpy3DPeer_ptds export
+0x00330910 cuMemcpyAsync_ptsz export
+0x00330930 cuMemcpyPeerAsync_ptsz export
+0x00330950 cuMemcpyHtoDAsync_v2_ptsz export
+0x00330970 cuMemcpyDtoHAsync_v2_ptsz export
+0x00330990 cuMemcpyDtoDAsync_v2_ptsz export
+0x003309b0 cuMemcpyHtoAAsync_v2_ptsz export
+0x003309d0 cuMemcpyAtoHAsync_v2_ptsz export
+0x003309f0 cuMemcpy2DAsync_v2_ptsz export
+0x00330a10 cuMemcpy3DAsync_v2_ptsz export
+0x00330a30 cuMemcpy3DPeerAsync_ptsz export
+0x00330a50 cuMemcpyBatchAsync_ptsz export
+0x00330a70 cuMemcpy3DBatchAsync_ptsz export
+0x00330a90 cuMemsetD8_v2_ptds export
+0x00330ac0 cuMemsetD16_v2_ptds export
+0x00330ae0 cuMemsetD32_v2_ptds export
+0x00330b00 cuMemsetD2D8_v2_ptds export
+0x00330b20 cuMemsetD2D16_v2_ptds export
+0x00330b40 cuMemsetD2D32_v2_ptds export
+0x00330b60 cuMemsetD8Async_ptsz export
+0x00330b90 cuMemsetD16Async_ptsz export
+0x00330bb0 cuMemsetD32Async_ptsz export
+0x00330bd0 cuMemsetD2D8Async_ptsz export
+0x00330bf0 cuMemsetD2D16Async_ptsz export
+0x00330c10 cuMemsetD2D32Async_ptsz export
+0x00330c30 cuArrayCreate_v2 export
+0x00330c50 cuArrayGetDescriptor_v2 export
+0x00330c70 cuArrayGetSparseProperties export
+0x00330c90 cuMipmappedArrayGetSparseProperties export
+0x00330cb0 cuArrayGetMemoryRequirements export
+0x00330cd0 cuMipmappedArrayGetMemoryRequirements export
+0x00330cf0 cuArrayGetPlane export
+0x00330d10 cuArrayDestroy export
+0x00330d30 cuArray3DCreate_v2 export
+0x00330d50 cuArray3DGetDescriptor_v2 export
+0x00330d70 cuMipmappedArrayCreate export
+0x00330d90 cuMipmappedArrayGetLevel export
+0x00330db0 cuMipmappedArrayDestroy export
+0x00330dd0 cuMemGetHandleForAddressRange export
+0x00330df0 cuMemBatchDecompressAsync_ptsz export
+0x00330e10 cuMemAddressReserve export
+0x00330e30 cuMemAddressFree export
+0x00330e50 cuMemCreate export
+0x00330e70 cuMemRelease export
+0x00330e90 cuMemMap export
+0x00330eb0 cuMemMapArrayAsync_ptsz export
+0x00330ed0 cuMemUnmap export
+0x00330ef0 cuMemSetAccess export
+0x00330f10 cuMemGetAccess export
+0x00330f30 cuMemExportToShareableHandle export
+0x00330f50 cuMemImportFromShareableHandle export
+0x00330f70 cuMemGetAllocationGranularity export
+0x00330f90 cuMemGetAllocationPropertiesFromHandle export
+0x00330fb0 cuMemRetainAllocationHandle export
+0x00330fd0 cuMemFreeAsync_ptsz export
+0x00330ff0 cuMemAllocAsync_ptsz export
+0x00331010 cuMemPoolTrimTo export
+0x00331030 cuMemPoolSetAttribute export
+0x00331050 cuMemPoolGetAttribute export
+0x00331070 cuMemPoolSetAccess export
+0x00331090 cuMemPoolGetAccess export
+0x003310b0 cuMemPoolCreate export
+0x003310d0 cuMemPoolDestroy export
+0x003310f0 cuMemAllocFromPoolAsync_ptsz export
+0x00331110 cuMemPoolExportToShareableHandle export
+0x00331130 cuMemPoolImportFromShareableHandle export
+0x00331150 cuMemPoolExportPointer export
+0x00331170 cuMemPoolImportPointer export
+0x00331190 cuMulticastCreate export
+0x003311b0 cuMulticastAddDevice export
+0x003311d0 cuMulticastBindMem export
+0x003311f0 cuMulticastBindAddr export
+0x00331210 cuMulticastUnbind export
+0x00331230 cuMulticastGetGranularity export
+0x00331250 cuPointerGetAttribute export
+0x00331270 cuMemPrefetchAsync_ptsz export
+0x00331290 cuMemPrefetchAsync_v2_ptsz export
+0x003312b0 cuMemAdvise export
+0x003312d0 cuMemAdvise_v2 export
+0x003312f0 cuMemRangeGetAttribute export
+0x00331310 cuMemRangeGetAttributes export
+0x00331330 cuPointerSetAttribute export
+0x00331350 cuPointerGetAttributes export
+0x00331370 cuStreamCreate export
+0x00331390 cuStreamCreateWithPriority export
+0x003313b0 cuStreamGetPriority_ptsz export
+0x003313d0 cuStreamGetDevice_ptsz export
+0x003313f0 cuStreamGetFlags_ptsz export
+0x00331410 cuStreamGetId_ptsz export
+0x00331430 cuStreamGetCtx_ptsz export
+0x00331450 cuStreamGetCtx_v2_ptsz export
+0x00331470 cuStreamWaitEvent_ptsz export
+0x00331490 cuStreamAddCallback_ptsz export
+0x003314b0 cuStreamBeginCapture_v2_ptsz export
+0x003314d0 cuStreamBeginCaptureToGraph_ptsz export
+0x003314f0 cuThreadExchangeStreamCaptureMode export
+0x00331510 cuStreamEndCapture_ptsz export
+0x00331530 cuStreamIsCapturing_ptsz export
+0x00331550 cuStreamGetCaptureInfo_v2_ptsz export
+0x00331570 cuStreamGetCaptureInfo_v3_ptsz export
+0x00331590 cuStreamUpdateCaptureDependencies_ptsz export
+0x003315b0 cuStreamUpdateCaptureDependencies_v2_ptsz export
+0x003315d0 cuStreamAttachMemAsync_ptsz export
+0x003315f0 cuStreamQuery_ptsz export
+0x00331610 cuStreamSynchronize_ptsz export
+0x00331630 cuStreamDestroy_v2 export
+0x00331650 cuStreamCopyAttributes_ptsz export
+0x00331670 cuStreamGetAttribute_ptsz export
+0x00331690 cuStreamSetAttribute_ptsz export
+0x003316b0 cuEventCreate export
+0x003316d0 cuEventRecord_ptsz export
+0x003316f0 cuEventRecordWithFlags_ptsz export
+0x00331710 cuEventQuery export
+0x00331730 cuEventSynchronize export
+0x00331750 cuEventDestroy_v2 export
+0x00331770 cuEventElapsedTime export
+0x00331790 cuEventElapsedTime_v2 export
+0x003317b0 cuImportExternalMemory export
+0x003317d0 cuExternalMemoryGetMappedBuffer export
+0x003317f0 cuExternalMemoryGetMappedMipmappedArray export
+0x00331810 cuDestroyExternalMemory export
+0x00331830 cuImportExternalSemaphore export
+0x00331850 cuSignalExternalSemaphoresAsync_ptsz export
+0x00331870 cuWaitExternalSemaphoresAsync_ptsz export
+0x00331890 cuDestroyExternalSemaphore export
+0x003318b0 cuStreamWaitValue32_v2_ptsz export
+0x003318d0 cuStreamWaitValue64_v2_ptsz export
+0x003318f0 cuStreamWriteValue32_v2_ptsz export
+0x00331910 cuStreamWriteValue64_v2_ptsz export
+0x00331930 cuStreamBatchMemOp_v2_ptsz export
+0x00331950 cuFuncGetAttribute export
+0x00331970 cuFuncSetAttribute export
+0x00331990 cuFuncSetCacheConfig export
+0x003319b0 cuFuncGetModule export
+0x003319d0 cuFuncGetName export
+0x003319f0 cuFuncGetParamInfo export
+0x00331a10 cuFuncIsLoaded export
+0x00331a30 cuFuncLoad export
+0x00331a50 cuLaunchKernel_ptsz export
+0x00331a70 cuLaunchKernelEx_ptsz export
+0x00331a90 cuLaunchCooperativeKernel_ptsz export
+0x00331ab0 cuLaunchCooperativeKernelMultiDevice export
+0x00331ad0 cuLaunchHostFunc_ptsz export
+0x00331af0 cuFuncSetBlockShape export
+0x00331b10 cuFuncSetSharedSize export
+0x00331b30 cuParamSetSize export
+0x00331b50 cuParamSeti export
+0x00331b70 cuParamSetf export
+0x00331b90 cuParamSetv export
+0x00331bb0 cuLaunch export
+0x00331bd0 cuLaunchGrid export
+0x00331bf0 cuLaunchGridAsync export
+0x00331c10 cuParamSetTexRef export
+0x00331c30 cuFuncSetSharedMemConfig export
+0x00331c50 cuGraphCreate export
+0x00331c70 cuGraphAddKernelNode_v2 export
+0x0034f650 cuGraphKernelNodeGetParams_v2 export
+0x0034f670 cuGraphKernelNodeSetParams_v2 export
+0x0034f690 cuGraphAddMemcpyNode export
+0x0034f6b0 cuGraphMemcpyNodeGetParams export
+0x0034f6d0 cuGraphMemcpyNodeSetParams export
+0x0034f6f0 cuGraphAddMemsetNode export
+0x0034f710 cuGraphMemsetNodeGetParams export
+0x0034f730 cuGraphMemsetNodeSetParams export
+0x0034f750 cuGraphAddHostNode export
+0x0034f770 cuGraphHostNodeGetParams export
+0x0034f790 cuGraphHostNodeSetParams export
+0x0034f7b0 cuGraphAddChildGraphNode export
+0x0034f7d0 cuGraphChildGraphNodeGetGraph export
+0x0034f7f0 cuGraphAddEmptyNode export
+0x0034f810 cuGraphAddEventRecordNode export
+0x0034f830 cuGraphEventRecordNodeGetEvent export
+0x0034f850 cuGraphEventRecordNodeSetEvent export
+0x0034f870 cuGraphAddEventWaitNode export
+0x0034f890 cuGraphEventWaitNodeGetEvent export
+0x0034f8b0 cuGraphEventWaitNodeSetEvent export
+0x0034f8d0 cuGraphAddExternalSemaphoresSignalNode export
+0x0034f8f0 cuGraphExternalSemaphoresSignalNodeGetParams export
+0x0034f910 cuGraphExternalSemaphoresSignalNodeSetParams export
+0x0034f930 cuGraphAddExternalSemaphoresWaitNode export
+0x0034f950 cuGraphExternalSemaphoresWaitNodeGetParams export
+0x0034f970 cuGraphExternalSemaphoresWaitNodeSetParams export
+0x0034f990 cuGraphAddBatchMemOpNode export
+0x0034f9b0 cuGraphBatchMemOpNodeGetParams export
+0x0034f9d0 cuGraphBatchMemOpNodeSetParams export
+0x0034f9f0 cuGraphExecBatchMemOpNodeSetParams export
+0x0034fa10 cuGraphAddMemAllocNode export
+0x0034fa30 cuGraphMemAllocNodeGetParams export
+0x0034fa50 cuGraphAddMemFreeNode export
+0x0034fa70 cuGraphMemFreeNodeGetParams export
+0x0034fa90 cuDeviceGraphMemTrim export
+0x0034fab0 cuDeviceGetGraphMemAttribute export
+0x0034fad0 cuDeviceSetGraphMemAttribute export
+0x0034faf0 cuGraphClone export
+0x0034fb10 cuGraphNodeFindInClone export
+0x0034fb30 cuGraphNodeGetType export
+0x0034fb50 cuGraphGetNodes export
+0x0034fb70 cuGraphGetRootNodes export
+0x0034fb90 cuGraphGetEdges export
+0x0034fbb0 cuGraphGetEdges_v2 export
+0x0034fbd0 cuGraphNodeGetDependencies export
+0x0034fbf0 cuGraphNodeGetDependencies_v2 export
+0x0034fc10 cuGraphNodeGetDependentNodes export
+0x0034fc30 cuGraphNodeGetDependentNodes_v2 export
+0x0034fc50 cuGraphAddDependencies export
+0x0034fc70 cuGraphAddDependencies_v2 export
+0x0034fc90 cuGraphRemoveDependencies export
+0x0034fcb0 cuGraphRemoveDependencies_v2 export
+0x0034fcd0 cuGraphDestroyNode export
+0x0034fcf0 cuGraphInstantiateWithFlags export
+0x0034fd10 cuGraphInstantiateWithParams_ptsz export
+0x0034fd30 cuGraphExecGetFlags export
+0x0034fd50 cuGraphExecKernelNodeSetParams_v2 export
+0x0034fd70 cuGraphExecMemcpyNodeSetParams export
+0x0034fd90 cuGraphExecMemsetNodeSetParams export
+0x0034fdb0 cuGraphExecHostNodeSetParams export
+0x0034fdd0 cuGraphExecChildGraphNodeSetParams export
+0x0034fdf0 cuGraphExecEventRecordNodeSetEvent export
+0x0034fe10 cuGraphExecEventWaitNodeSetEvent export
+0x0034fe30 cuGraphExecExternalSemaphoresSignalNodeSetParams export
+0x0034fe50 cuGraphExecExternalSemaphoresWaitNodeSetParams export
+0x0034fe70 cuGraphNodeSetEnabled export
+0x0034fe90 cuGraphNodeGetEnabled export
+0x0034feb0 cuGraphUpload_ptsz export
+0x0034fed0 cuGraphLaunch_ptsz export
+0x0034fef0 cuGraphExecDestroy export
+0x0034ff10 cuGraphDestroy export
+0x0034ff30 cuGraphExecUpdate_v2 export
+0x0034ff50 cuGraphKernelNodeCopyAttributes export
+0x0034ff70 cuGraphKernelNodeGetAttribute export
+0x0034ff90 cuGraphKernelNodeSetAttribute export
+0x0034ffb0 cuGraphDebugDotPrint export
+0x0034ffd0 cuUserObjectCreate export
+0x0034fff0 cuUserObjectRetain export
+0x00350010 cuUserObjectRelease export
+0x00350030 cuGraphRetainUserObject export
+0x00350050 cuGraphReleaseUserObject export
+0x00350070 cuGraphAddNode export
+0x00350090 cuGraphAddNode_v2 export
+0x003500b0 cuGraphNodeSetParams export
+0x003500d0 cuGraphExecNodeSetParams export
+0x003500f0 cuGraphConditionalHandleCreate export
+0x00350110 cuOccupancyMaxActiveBlocksPerMultiprocessor export
+0x00350130 cuOccupancyMaxActiveBlocksPerMultiprocessorWithFlags export
+0x00350150 cuOccupancyMaxPotentialBlockSize export
+0x00350170 cuOccupancyMaxPotentialBlockSizeWithFlags export
+0x00350190 cuOccupancyAvailableDynamicSMemPerBlock export
+0x003501b0 cuOccupancyMaxPotentialClusterSize export
+0x003501d0 cuOccupancyMaxActiveClusters export
+0x003501f0 cuTexRefSetArray export
+0x00350210 cuTexRefSetMipmappedArray export
+0x00350230 cuTexRefSetAddress_v2 export
+0x00350250 cuTexRefSetAddress2D_v3 export
+0x00350270 cuTexRefSetFormat export
+0x00350290 cuTexRefSetAddressMode export
+0x003502b0 cuTexRefSetFilterMode export
+0x003502d0 cuTexRefSetMipmapFilterMode export
+0x003502f0 cuTexRefSetMipmapLevelBias export
+0x00350310 cuTexRefSetMipmapLevelClamp export
+0x00350330 cuTexRefSetMaxAnisotropy export
+0x00350350 cuTexRefSetBorderColor export
+0x00350370 cuTexRefSetFlags export
+0x00350390 cuTexRefGetAddress_v2 export
+0x003503b0 cuTexRefGetArray export
+0x003503d0 cuTexRefGetMipmappedArray export
+0x003503f0 cuTexRefGetAddressMode export
+0x00350410 cuTexRefGetFilterMode export
+0x00350430 cuTexRefGetFormat export
+0x00350450 cuTexRefGetMipmapFilterMode export
+0x00350470 cuTexRefGetMipmapLevelBias export
+0x00350490 cuTexRefGetMipmapLevelClamp export
+0x003504b0 cuTexRefGetMaxAnisotropy export
+0x003504d0 cuTexRefGetBorderColor export
+0x003504f0 cuTexRefGetFlags export
+0x00350510 cuTexRefCreate export
+0x00350530 cuTexRefDestroy export
+0x00350550 cuSurfRefSetArray export
+0x00350570 cuSurfRefGetArray export
+0x00350590 cuTexObjectCreate export
+0x003505b0 cuTexObjectDestroy export
+0x003505d0 cuTexObjectGetResourceDesc export
+0x003505f0 cuTexObjectGetTextureDesc export
+0x00350610 cuTexObjectGetResourceViewDesc export
+0x00350630 cuSurfObjectCreate export
+0x00350650 cuSurfObjectDestroy export
+0x00350670 cuSurfObjectGetResourceDesc export
+0x00350690 cuTensorMapEncodeTiled export
+0x003506b0 cuTensorMapEncodeIm2col export
+0x003506d0 cuTensorMapEncodeIm2colWide export
+0x003506f0 cuTensorMapReplaceAddress export
+0x00350710 cuDeviceCanAccessPeer export
+0x00350730 cuCtxEnablePeerAccess export
+0x00350750 cuCtxDisablePeerAccess export
+0x00350770 cuDeviceGetP2PAttribute export
+0x00350790 cuGraphicsUnregisterResource export
+0x003507b0 cuGraphicsSubResourceGetMappedArray export
+0x003507d0 cuGraphicsResourceGetMappedMipmappedArray export
+0x003507f0 cuGraphicsResourceGetMappedPointer_v2 export
+0x00350810 cuGraphicsResourceSetMapFlags_v2 export
+0x00350830 cuGraphicsMapResources_ptsz export
+0x00350850 cuGraphicsUnmapResources_ptsz export
+0x00350870 cuGetProcAddress_v2 export
+0x00350890 cuCoredumpGetAttribute export
+0x003508b0 cuCoredumpGetAttributeGlobal export
+0x003508d0 cuCoredumpSetAttribute export
+0x003508f0 cuCoredumpSetAttributeGlobal export
+0x00350910 cuGetExportTable export
+0x00350930 cuGreenCtxCreate export
+0x00350950 cuGreenCtxDestroy export
+0x00350970 cuCtxFromGreenCtx export
+0x00350990 cuDeviceGetDevResource export
+0x003509b0 cuCtxGetDevResource export
+0x003509d0 cuGreenCtxGetDevResource export
+0x003509f0 cuDevSmResourceSplitByCount export
+0x00350a10 cuDevResourceGenerateDesc export
+0x00350a30 cuGreenCtxRecordEvent export
+0x00350a50 cuGreenCtxWaitEvent export
+0x00350a70 cuStreamGetGreenCtx export
+0x00350a90 cuGreenCtxStreamCreate export
+0x00350ab0 cuMemHostRegister export
+0x00350ad0 cuGraphicsResourceSetMapFlags export
+0x00350af0 cuLinkCreate export
+0x00350b10 cuLinkAddData export
+0x00350b30 cuLinkAddFile export
+0x00350b50 cuTexRefSetAddress2D_v2 export
+0x00350b70 cuDeviceTotalMem export
+0x00350b90 cuCtxCreate export
+0x00350bb0 cuModuleGetGlobal export
+0x0036e7b0 cuMemGetInfo export
+0x0036e7d0 cuMemAlloc export
+0x0036e7f0 cuMemAllocPitch export
+0x0036e810 cuMemFree export
+0x0036e830 cuMemGetAddressRange export
+0x0036e850 cuMemAllocHost export
+0x0036e870 cuMemHostGetDevicePointer export
+0x0036e890 cuMemcpyHtoD export
+0x0036e8b0 cuMemcpyDtoH export
+0x0036e8d0 cuMemcpyDtoD export
+0x0036e8f0 cuMemcpyDtoA export
+0x0036e910 cuMemcpyAtoD export
+0x0036e930 cuMemcpyHtoA export
+0x0036e950 cuMemcpyAtoH export
+0x0036e970 cuMemcpyAtoA export
+0x0036e990 cuMemcpyHtoAAsync export
+0x0036e9b0 cuMemcpyAtoHAsync export
+0x0036e9d0 cuMemcpy2D export
+0x0036e9f0 cuMemcpy2DUnaligned export
+0x0036ea10 cuMemcpy3D export
+0x0036ea30 cuMemcpyHtoDAsync export
+0x0036ea50 cuMemcpyDtoHAsync export
+0x0036ea70 cuMemcpyDtoDAsync export
+0x0036ea90 cuMemcpy2DAsync export
+0x0036eab0 cuMemcpy3DAsync export
+0x0036ead0 cuMemsetD8 export
+0x0036eb00 cuMemsetD16 export
+0x0036eb20 cuMemsetD32 export
+0x0036eb40 cuMemsetD2D8 export
+0x0036eb60 cuMemsetD2D16 export
+0x0036eb80 cuMemsetD2D32 export
+0x0036eba0 cuArrayCreate export
+0x0036ebc0 cuArrayGetDescriptor export
+0x0036ebe0 cuArray3DCreate export
+0x0036ec00 cuArray3DGetDescriptor export
+0x0036ec20 cuTexRefSetAddress export
+0x0036ec40 cuTexRefSetAddress2D export
+0x0036ec60 cuTexRefGetAddress export
+0x0036ec80 cuGraphicsResourceGetMappedPointer export
+0x0036eca0 cuCtxDestroy export
+0x0036ecc0 cuCtxPopCurrent export
+0x0036ece0 cuCtxPushCurrent export
+0x0036ed00 cuStreamDestroy export
+0x0036ed20 cuEventDestroy export
+0x0036ed40 cuDevicePrimaryCtxRelease export
+0x0036ed60 cuDevicePrimaryCtxReset export
+0x0036ed80 cuDevicePrimaryCtxSetFlags export
+0x0036eda0 cuMemcpyHtoD_v2 export
+0x0036edc0 cuMemcpyDtoH_v2 export
+0x0036ede0 cuMemcpyDtoD_v2 export
+0x0036ee00 cuMemcpyDtoA_v2 export
+0x0036ee20 cuMemcpyAtoD_v2 export
+0x0036ee40 cuMemcpyHtoA_v2 export
+0x0036ee60 cuMemcpyAtoH_v2 export
+0x0036ee80 cuMemcpyAtoA_v2 export
+0x0036eea0 cuMemcpyHtoAAsync_v2 export
+0x0036eec0 cuMemcpyAtoHAsync_v2 export
+0x0036eee0 cuMemcpy2D_v2 export
+0x0036ef00 cuMemcpy2DUnaligned_v2 export
+0x0036ef20 cuMemcpy3D_v2 export
+0x0036ef40 cuMemcpyHtoDAsync_v2 export
+0x0036ef60 cuMemcpyDtoHAsync_v2 export
+0x0036ef80 cuMemcpyDtoDAsync_v2 export
+0x0036efa0 cuMemcpy2DAsync_v2 export
+0x0036efc0 cuMemcpy3DAsync_v2 export
+0x0036efe0 cuMemsetD8_v2 export
+0x0036f010 cuMemsetD16_v2 export
+0x0036f030 cuMemsetD32_v2 export
+0x0036f050 cuMemsetD2D8_v2 export
+0x0036f070 cuMemsetD2D16_v2 export
+0x0036f090 cuMemsetD2D32_v2 export
+0x0036f0b0 cuMemcpy export
+0x0036f0d0 cuMemcpyAsync export
+0x0036f0f0 cuMemcpyPeer export
+0x0036f110 cuMemcpyPeerAsync export
+0x0036f130 cuMemcpy3DPeer export
+0x0036f150 cuMemcpy3DPeerAsync export
+0x0036f170 cuMemcpyBatchAsync export
+0x0036f190 cuMemcpy3DBatchAsync export
+0x0036f1b0 cuMemsetD8Async export
+0x0036f1e0 cuMemsetD16Async export
+0x0036f200 cuMemsetD32Async export
+0x0036f220 cuMemsetD2D8Async export
+0x0036f240 cuMemsetD2D16Async export
+0x0036f260 cuMemsetD2D32Async export
+0x0036f280 cuStreamGetPriority export
+0x0036f2a0 cuStreamGetId export
+0x0036f2c0 cuStreamGetFlags export
+0x0036f2e0 cuStreamGetDevice export
+0x0036f300 cuStreamGetCtx export
+0x0036f320 cuStreamGetCtx_v2 export
+0x0036f340 cuStreamWaitEvent export
+0x0036f360 cuStreamAddCallback export
+0x0036f380 cuStreamAttachMemAsync export
+0x0036f3a0 cuStreamQuery export
+0x0036f3c0 cuStreamSynchronize export
+0x0036f3e0 cuEventRecord export
+0x0036f400 cuEventRecordWithFlags export
+0x0036f420 cuLaunchKernel export
+0x0036f440 cuLaunchKernelEx export
+0x0036f460 cuLaunchHostFunc export
+0x0036f480 cuGraphicsMapResources export
+0x0036f4a0 cuGraphicsUnmapResources export
+0x0036f4c0 cuStreamWriteValue32 export
+0x0036f4e0 cuStreamWaitValue32 export
+0x0036f500 cuStreamWriteValue64 export
+0x0036f520 cuStreamWaitValue64 export
+0x0036f540 cuStreamBatchMemOp export
+0x0036f560 cuStreamWriteValue32_ptsz export
+0x0036f580 cuStreamWaitValue32_ptsz export
+0x0036f5a0 cuStreamWriteValue64_ptsz export
+0x0036f5c0 cuStreamWaitValue64_ptsz export
+0x0036f5e0 cuStreamBatchMemOp_ptsz export
+0x0036f600 cuStreamWriteValue32_v2 export
+0x0036f620 cuStreamWaitValue32_v2 export
+0x0036f640 cuStreamWriteValue64_v2 export
+0x0036f660 cuStreamWaitValue64_v2 export
+0x0036f680 cuStreamBatchMemOp_v2 export
+0x0036f6a0 cuMemPrefetchAsync export
+0x0036f6c0 cuMemPrefetchAsync_v2 export
+0x0036f6e0 cuLaunchCooperativeKernel export
+0x0036f700 cuSignalExternalSemaphoresAsync export
+0x0036f720 cuWaitExternalSemaphoresAsync export
+0x0036f740 cuStreamBeginCapture export
+0x0036f760 cuStreamBeginCapture_ptsz export
+0x0036f780 cuStreamBeginCapture_v2 export
+0x0036f7a0 cuStreamBeginCaptureToGraph export
+0x0036f7c0 cuStreamEndCapture export
+0x0036f7e0 cuStreamIsCapturing export
+0x0036f800 cuStreamGetCaptureInfo export
+0x0036f820 cuStreamGetCaptureInfo_ptsz export
+0x0036f840 cuStreamGetCaptureInfo_v2 export
+0x0036f860 cuStreamGetCaptureInfo_v3 export
+0x0036f880 cuGraphAddKernelNode export
+0x0036f8a0 cuGraphKernelNodeGetParams export
+0x0036f8c0 cuGraphKernelNodeSetParams export
+0x0036f8e0 cuGraphExecKernelNodeSetParams export
+0x0036f900 cuGraphInstantiateWithParams export
+0x0036f920 cuGraphExecUpdate export
+0x0036f940 cuGraphUpload export
+0x0036f960 cuGraphLaunch export
+0x0036f980 cuStreamCopyAttributes export
+0x0036f9a0 cuStreamGetAttribute export
+0x0036f9c0 cuStreamSetAttribute export
+0x0036f9e0 cuIpcOpenMemHandle export
+0x0036fa00 cuGraphInstantiate export
+0x0036fa20 cuGraphInstantiate_v2 export
+0x0036fa40 cuMemMapArrayAsync export
+0x0036fa60 cuMemFreeAsync export
+0x0036fa80 cuMemAllocAsync export
+0x0036faa0 cuMemAllocFromPoolAsync export
+0x0036fac0 cuStreamUpdateCaptureDependencies export
+0x0036fae0 cuStreamUpdateCaptureDependencies_v2 export
+0x0036fb00 cuMemBatchDecompressAsync export
+0x0036fb20 cuGetProcAddress export
+0x0036fb40 cuCheckpointProcessGetRestoreThreadId export
+0x0036fb60 cuCheckpointProcessGetState export
+0x0036fb80 cuCheckpointProcessLock export
+0x0036fba0 cuCheckpointProcessCheckpoint export
+0x0036fbc0 cuCheckpointProcessRestore export
+0x0036fbe0 cuCheckpointProcessUnlock export
+0x0036fc00 cuGraphicsEGLRegisterImage export
+0x0036fc20 cuEGLStreamConsumerConnect export
+0x0036fc40 cuEGLStreamConsumerConnectWithFlags export
+0x0036fc60 cuEGLStreamConsumerDisconnect export
+0x0036fc80 cuEGLStreamConsumerAcquireFrame export
+0x0036fca0 cuEGLStreamConsumerReleaseFrame export
+0x0036fcc0 cuEGLStreamProducerConnect export
+0x0036fce0 cuEGLStreamProducerDisconnect export
+0x0036fd00 cuEGLStreamProducerPresentFrame export
+0x0036fd20 cuEGLStreamProducerReturnFrame export
+0x0036fd40 cuGraphicsResourceGetMappedEglFrame export
+0x0036fd60 cuGraphicsGLRegisterBuffer export
+0x0036fd80 cuGraphicsGLRegisterImage export
+0x0036fda0 cuGLGetDevices_v2 export
+0x0036fdc0 cuGLCtxCreate_v2 export
+0x0036fde0 cuGLInit export
+0x0036fe00 cuGLRegisterBufferObject export
+0x0036fe20 cuGLMapBufferObject_v2_ptds export
+0x0036fe40 cuGLUnmapBufferObject export
+0x0036fe60 cuGLUnregisterBufferObject export
+0x0036fe80 cuGLSetBufferObjectMapFlags export
+0x0036fea0 cuGLMapBufferObjectAsync_v2_ptsz export
+0x0036fec0 cuGLUnmapBufferObjectAsync export
+0x0036fee0 cuGLGetDevices export
+0x0036ff00 cuGLMapBufferObject_v2 export
+0x0036ff20 cuGLMapBufferObjectAsync_v2 export
+0x0038d820 cuGLCtxCreate export
+0x0038d840 cuGLMapBufferObject export
+0x0038d860 cuGLMapBufferObjectAsync export
+0x0038d880 cuProfilerInitialize export
+0x0038d8a0 cuProfilerStart export
+0x0038d8c0 cuProfilerStop export
+0x0038d8e0 cuVDPAUGetDevice export
+0x0038d900 cuVDPAUCtxCreate_v2 export
+0x0038d920 cuGraphicsVDPAURegisterVideoSurface export
+0x0038d940 cuGraphicsVDPAURegisterOutputSurface export
+0x0038d960 cuVDPAUCtxCreate export
+0x00487710 cudbgMain export
+#
+# --- generated wrappers (initial interposition slot targets) ---
+0x0036e2c0 wrapper_cuModuleGetGlobal wrapper
+0x003225e0 wrapper_cuCtxGetFlags wrapper
+0x00371570 wrapper_cuMemGetInfo wrapper
+0x0034b020 wrapper_cuFuncGetAttribute wrapper
+0x0037e6a0 wrapper_cuMemcpyAsync wrapper
+0x0037c8b0 wrapper_cuMemcpyDtoA_v2 wrapper
+0x00375390 wrapper_cuMemsetD32Async wrapper
+0x00385b60 wrapper_cuGraphExecKernelNodeSetParams wrapper
+0x003240f0 wrapper_cuCtxSetCacheConfig wrapper
+0x0034c8d0 wrapper_cuLaunchKernelEx_ptsz wrapper
+0x00344640 wrapper_cuPointerSetAttribute wrapper
+0x0034a240 wrapper_cuDestroyExternalSemaphore wrapper
+0x003270a0 wrapper_cuLibraryLoadFromFile wrapper
+0x00368b70 wrapper_cuDeviceCanAccessPeer wrapper
+0x00359120 wrapper_cuGraphAddExternalSemaphoresWaitNode wrapper
+0x00353810 wrapper_cuOccupancyMaxActiveClusters wrapper
+0x0035f6a0 wrapper_cuGraphExecUpdate_v2 wrapper
+0x00340590 wrapper_cuThreadExchangeStreamCaptureMode wrapper
+0x00358620 wrapper_cuGraphAddEventRecordNode wrapper
+0x0035c060 wrapper_cuGraphGetEdges wrapper
+0x0034da70 wrapper_cuFuncSetBlockShape wrapper
+0x0034ceb0 wrapper_cuLaunchCooperativeKernelMultiDevice wrapper
+0x00366510 wrapper_cuTensorMapEncodeTiled wrapper
+0x0031f700 wrapper_cuCtxGetExecAffinity wrapper
+0x00369cc0 wrapper_cuGraphicsResourceGetMappedPointer_v2 wrapper
+0x0035e3c0 wrapper_cuGraphExecChildGraphNodeSetParams wrapper
+0x003939c0 wrapper_cuGLMapBufferObjectAsync wrapper
+0x003324b0 wrapper_cuFuncGetParamInfo wrapper
+0x003369f0 wrapper_cuMemcpyAtoA_v2_ptds wrapper
+0x00342000 wrapper_cuMemPoolExportToShareableHandle wrapper
+0x003682a0 wrapper_cuSurfObjectGetResourceDesc wrapper
+0x0031d160 wrapper_cuModuleGetLoadingMode wrapper
+0x003678e0 wrapper_cuTexObjectGetResourceDesc wrapper
+0x0033f640 wrapper_cuMemUnmap wrapper
+0x003275f0 wrapper_cuLibraryGetKernel wrapper
+0x0038cab0 wrapper_cuGLUnmapBufferObject wrapper
+0x00389830 wrapper_cuEGLStreamConsumerConnectWithFlags wrapper
+0x0036c810 wrapper_cuGreenCtxRecordEvent wrapper
+0x0031acd0 wrapper_cuModuleEnumerateFunctions wrapper
+0x00349e40 wrapper_cuSignalExternalSemaphoresAsync_ptsz wrapper
+0x0031d570 wrapper_cuMemGetInfo_v2 wrapper
+0x00364330 wrapper_cuTexRefSetBorderColor wrapper
+0x00394b80 wrapper_cuGraphicsVDPAURegisterOutputSurface wrapper
+0x0033b7a0 wrapper_cuMipmappedArrayGetLevel wrapper
+0x00341620 wrapper_cuMemPoolGetAttribute wrapper
+0x0031b1f0 wrapper_cuKernelGetName wrapper
+0x0037a2f0 wrapper_cuStreamGetCtx wrapper
+0x00323e70 wrapper_cuCtxGetSharedMemConfig wrapper
+0x0038b170 wrapper_cuGraphicsGLRegisterBuffer wrapper
+0x00348360 wrapper_cuEventQuery wrapper
+0x003598e0 wrapper_cuGraphBatchMemOpNodeSetParams wrapper
+0x00371ae0 wrapper_cuMemAlloc wrapper
+0x00383f60 wrapper_cuSignalExternalSemaphoresAsync wrapper
+0x0035f460 wrapper_cuGraphDestroy wrapper
+0x00381e60 wrapper_cuStreamBatchMemOp_v2 wrapper
+0x00368510 wrapper_cuTexObjectDestroy wrapper
+0x00343cd0 wrapper_cuMemPrefetchAsync_ptsz wrapper
+0x00337e60 wrapper_cuMemcpyAtoHAsync_v2_ptsz wrapper
+0x00374bd0 wrapper_cuMemcpy2DAsync wrapper
+0x00331c90 wrapper_cuMemRangeGetAttributes wrapper
+0x00363300 wrapper_cuTexRefSetAddressMode wrapper
+0x00322ef0 wrapper_cuModuleGetSurfRef wrapper
+0x0035aaf0 wrapper_cuGraphNodeGetEnabled wrapper
+0x0035e680 wrapper_cuGraphNodeSetEnabled wrapper
+0x00349270 wrapper_cuImportExternalMemory wrapper
+0x0035cf40 wrapper_cuGraphNodeGetDependentNodes_v2 wrapper
+0x00369700 wrapper_cuGraphicsSubResourceGetMappedArray wrapper
+0x0033a9c0 wrapper_cuArray3DCreate_v2 wrapper
+0x00384160 wrapper_cuWaitExternalSemaphoresAsync wrapper
+0x0035b360 wrapper_cuGraphAddMemFreeNode wrapper
+0x00323230 wrapper_cuCtxSynchronize wrapper
+0x00336600 wrapper_cuMemcpyHtoA_v2_ptds wrapper
+0x0037b860 wrapper_cuEventDestroy wrapper
+0x0036a060 wrapper_cuGraphicsResourceSetMapFlags_v2 wrapper
+0x00358f30 wrapper_cuGraphExternalSemaphoresSignalNodeSetParams wrapper
+0x0033b0a0 wrapper_cuMipmappedArrayGetMemoryRequirements wrapper
+0x003265a0 wrapper_cuLinkAddFile_v2 wrapper
+0x00363db0 wrapper_cuTexRefSetMipmapLevelClamp wrapper
+0x0031a850 wrapper_cuDriverGetVersion wrapper
+0x0037af90 wrapper_cuStreamCopyAttributes wrapper
+0x00388cc0 wrapper_cuCheckpointProcessLock wrapper
+0x003322d0 wrapper_cuFuncGetName wrapper
+0x0037b5b0 wrapper_cuStreamDestroy wrapper
+0x0034a4b0 wrapper_cuStreamBatchMemOp_v2_ptsz wrapper
+0x00357cd0 wrapper_cuGraphAddHostNode wrapper
+0x003438e0 wrapper_cuMulticastBindAddr wrapper
+0x0035b050 wrapper_cuGraphAddMemAllocNode wrapper
+0x003693f0 wrapper_cuDeviceGetP2PAttribute wrapper
+0x0038c830 wrapper_cuGLMapBufferObjectAsync_v2 wrapper
+0x0035eb30 wrapper_cuGraphUpload_ptsz wrapper
+0x00379c30 wrapper_cuStreamGetId wrapper
+0x00324540 wrapper_cuCtxResetPersistingL2Cache wrapper
+0x0031bc10 wrapper_cuDeviceGetCount wrapper
+0x0035df50 wrapper_cuGraphExecKernelNodeSetParams_v2 wrapper
+0x00388f50 wrapper_cuCheckpointProcessCheckpoint wrapper
+0x003465b0 wrapper_cuStreamUpdateCaptureDependencies_ptsz wrapper
+0x0036d650 wrapper_cuLinkAddData wrapper
+0x003398b0 wrapper_cuMemsetD2D32Async_ptsz wrapper
+0x00341ab0 wrapper_cuMemPoolCreate wrapper
+0x00335a80 wrapper_cuMemcpyPeer_ptds wrapper
+0x003206d0 wrapper_cuCtxCreate_v2 wrapper
+0x00346860 wrapper_cuStreamEndCapture_ptsz wrapper
+0x00320a70 wrapper_cuCtxCreate_v3 wrapper
+0x00320f40 wrapper_cuCtxCreate_v4 wrapper
+0x003608c0 wrapper_cuGraphReleaseUserObject wrapper
+0x0035f1d0 wrapper_cuGraphExecDestroy wrapper
+0x00393230 wrapper_cuVDPAUCtxCreate wrapper
+0x00379670 wrapper_cuGraphicsUnmapResources wrapper
+0x00348ec0 wrapper_cuEventElapsedTime_v2 wrapper
+0x0035dbf0 wrapper_cuGraphExecGetFlags wrapper
+0x0031f9a0 wrapper_cuCtxAttach wrapper
+0x0031ff10 wrapper_cuDevicePrimaryCtxRelease_v2 wrapper
+0x00364b00 wrapper_cuTexRefGetMipmappedArray wrapper
+0x0036a2f0 wrapper_cuGraphicsMapResources_ptsz wrapper
+0x003816d0 wrapper_cuLaunchCooperativeKernel wrapper
+0x00365ab0 wrapper_cuTexRefGetMaxAnisotropy wrapper
+0x00337270 wrapper_cuMemcpyAsync_ptsz wrapper
+0x0033e540 wrapper_cuMemAddressReserve wrapper
+0x0035d7b0 wrapper_cuGraphInstantiateWithFlags wrapper
+0x0032a230 wrapper_cuMemAllocHost_v2 wrapper
+0x00369090 wrapper_cuCtxDisablePeerAccess wrapper
+0x00368db0 wrapper_cuCtxEnablePeerAccess wrapper
+0x003603b0 wrapper_cuUserObjectRetain wrapper
+0x003544f0 wrapper_cuDevSmResourceSplitByCount wrapper
+0x0033e070 wrapper_cuMemBatchDecompressAsync_ptsz wrapper
+0x0031aa10 wrapper_cuModuleGetFunctionCount wrapper
+0x0035cc40 wrapper_cuGraphNodeGetDependentNodes wrapper
+0x00342fb0 wrapper_cuMulticastUnbind wrapper
+0x00353bd0 wrapper_cuTexRefSetMipmappedArray wrapper
+0x0034dce0 wrapper_cuFuncSetSharedSize wrapper
+0x0037e890 wrapper_cuMemcpyPeer wrapper
+0x0035fef0 wrapper_cuGraphDebugDotPrint wrapper
+0x0036b2d0 wrapper_cuCoredumpGetAttributeGlobal wrapper
+0x00325460 wrapper_cuModuleUnload wrapper
+0x00342bc0 wrapper_cuMemPoolImportPointer wrapper
+0x0037dd60 wrapper_cuMemcpyDtoHAsync_v2 wrapper
+0x003449a0 wrapper_cuPointerGetAttributes wrapper
+0x003358a0 wrapper_cuMemcpy_ptds wrapper
+0x0031ef50 wrapper_cuFlushGPUDirectRDMAWrites wrapper
+0x0037e300 wrapper_cuMemcpy3DAsync_v2 wrapper
+0x0037e140 wrapper_cuMemcpy2DAsync_v2 wrapper
+0x00326250 wrapper_cuLinkAddData_v2 wrapper
+0x00388600 wrapper_cuGetProcAddress wrapper
+0x00353db0 wrapper_cuSurfRefSetArray wrapper
+0x0032a5d0 wrapper_cuMemFreeHost wrapper
+0x00365030 wrapper_cuTexRefGetFormat wrapper
+0x0036d190 wrapper_cuMemHostRegister wrapper
+0x003822c0 wrapper_cuStreamWaitValue32 wrapper
+0x00329830 wrapper_cuMemAlloc_v2 wrapper
+0x00343520 wrapper_cuMulticastCreate wrapper
+0x0037ce80 wrapper_cuMemcpyAtoH_v2 wrapper
+0x003514e0 wrapper_cuGraphEventWaitNodeGetEvent wrapper
+0x00338070 wrapper_cuMemcpy2DAsync_v2_ptsz wrapper
+0x00360b00 wrapper_cuGraphNodeSetParams wrapper
+0x00362b70 wrapper_cuTexRefSetAddress2D_v2 wrapper
+0x003626c0 wrapper_cuTexRefSetAddress2D_v3 wrapper
+0x00355070 wrapper_cuGraphMemcpyNodeGetParams wrapper
+0x003295d0 wrapper_cuKernelSetCacheConfig wrapper
+0x00367c60 wrapper_cuTexObjectGetTextureDesc wrapper
+0x0035b8e0 wrapper_cuDeviceGetGraphMemAttribute wrapper
+0x00346f90 wrapper_cuStreamAttachMemAsync_ptsz wrapper
+0x0035e8d0 wrapper_cuStreamGetGreenCtx wrapper
+0x00337c60 wrapper_cuMemcpyHtoAAsync_v2_ptsz wrapper
+0x003724c0 wrapper_cuMemAllocHost wrapper
+0x00325090 wrapper_cuModuleLoadDataEx wrapper
+0x003407f0 wrapper_cuMemAllocAsync_ptsz wrapper
+0x00336d90 wrapper_cuMemcpy2DUnaligned_v2_ptds wrapper
+0x00337a70 wrapper_cuMemcpyDtoDAsync_v2_ptsz wrapper
+0x003252a0 wrapper_cuModuleLoadFatBinary wrapper
+0x00381a40 wrapper_cuStreamBatchMemOp wrapper
+0x0033ae60 wrapper_cuArrayGetMemoryRequirements wrapper
+0x003367f0 wrapper_cuMemcpyAtoH_v2_ptds wrapper
+0x00333280 wrapper_cuDeviceUnregisterAsyncNotification wrapper
+0x00370310 wrapper_cuArrayGetDescriptor wrapper
+0x00358960 wrapper_cuGraphAddEventWaitNode wrapper
+0x0036bb70 wrapper_cuGreenCtxCreate wrapper
+0x00341070 wrapper_cuMemAllocFromPoolAsync_ptsz wrapper
+0x00343af0 wrapper_cuPointerGetAttribute wrapper
+0x00382050 wrapper_cuStreamWriteValue32 wrapper
+0x00384e10 wrapper_cuStreamBeginCaptureToGraph wrapper
+0x0034e480 wrapper_cuParamSetTexRef wrapper
+0x0038b4e0 wrapper_cuGraphicsGLRegisterImage wrapper
+0x0033c720 wrapper_cuMemGetHandleForAddressRange wrapper
+0x003858a0 wrapper_cuGraphKernelNodeSetParams wrapper
+0x00373480 wrapper_cuMemcpyHtoA wrapper
+0x0034adc0 wrapper_cuStreamWriteValue64_v2_ptsz wrapper
+0x0038ab50 wrapper_cuEGLStreamProducerReturnFrame wrapper
+0x00372b30 wrapper_cuMemcpyHtoD wrapper
+0x00373db0 wrapper_cuMemcpyAtoHAsync wrapper
+0x0036acb0 wrapper_cuGetProcAddress_v2 wrapper
+0x00382a10 wrapper_cuStreamWriteValue32_ptsz wrapper
+0x00334c40 wrapper_cuIpcGetMemHandle wrapper
+0x0035d2b0 wrapper_cuGetExportTable wrapper
+0x00389100 wrapper_cuCheckpointProcessRestore wrapper
+0x00363b20 wrapper_cuTexRefSetMipmapLevelBias wrapper
+0x00353f90 wrapper_cuTexObjectCreate wrapper
+0x00371f00 wrapper_cuMemFree wrapper
+0x00394800 wrapper_cuGraphicsVDPAURegisterVideoSurface wrapper
+0x00338b90 wrapper_cuMemcpy3DBatchAsync_ptsz wrapper
+0x00352bf0 wrapper_cuGraphExecMemcpyNodeSetParams wrapper
+0x00342800 wrapper_cuMemPoolExportPointer wrapper
+0x00383160 wrapper_cuStreamWaitValue64_ptsz wrapper
+0x00335c80 wrapper_cuMemcpyHtoD_v2_ptds wrapper
+0x0036d9a0 wrapper_cuLinkAddFile wrapper
+0x00386580 wrapper_cuGraphExecUpdate wrapper
+0x00379e80 wrapper_cuStreamGetFlags wrapper
+0x0035b6a0 wrapper_cuDeviceGraphMemTrim wrapper
+0x003217d0 wrapper_cuCtxDetach wrapper
+0x0035fc30 wrapper_cuGraphKernelNodeSetAttribute wrapper
+0x003699c0 wrapper_cuGraphicsResourceGetMappedMipmappedArray wrapper
+0x0034cb40 wrapper_cuLaunchCooperativeKernel_ptsz wrapper
+0x0037caa0 wrapper_cuMemcpyAtoD_v2 wrapper
+0x0038c350 wrapper_cuGLMapBufferObjectAsync_v2_ptsz wrapper
+0x00377e40 wrapper_cuTexRefSetAddress2D wrapper
+0x0038ce20 wrapper_cuGLUnmapBufferObjectAsync wrapper
+0x0033b550 wrapper_cuArray3DGetDescriptor_v2 wrapper
+0x00324310 wrapper_cuCtxSetSharedMemConfig wrapper
+0x0037a560 wrapper_cuStreamGetCtx_v2 wrapper
+0x00384b60 wrapper_cuStreamUpdateCaptureDependencies wrapper
+0x0036a9f0 wrapper_cuGraphicsResourceSetMapFlags wrapper
+0x0031ccb0 wrapper_cuCtxGetId wrapper
+0x00355430 wrapper_cuGraphChildGraphNodeGetGraph wrapper
+0x00355b30 wrapper_cuCtxFromGreenCtx wrapper
+0x0036be60 wrapper_cuGreenCtxDestroy wrapper
+0x00374d90 wrapper_cuMemcpy3DAsync wrapper
+0x00360f80 wrapper_cuGraphExecNodeSetParams wrapper
+0x0031bdf0 wrapper_cuDeviceGetName wrapper
+0x00326d30 wrapper_cuLibraryLoadData wrapper
+0x00335520 wrapper_cuMemHostRegister_v2 wrapper
+0x00327c10 wrapper_cuLibraryGetKernelCount wrapper
+0x00334180 wrapper_cuDeviceGetPCIBusId wrapper
+0x00323bf0 wrapper_cuCtxGetCacheConfig wrapper
+0x00355da0 wrapper_cuGraphAddMemcpyNode wrapper
+0x003268c0 wrapper_cuLinkComplete wrapper
+0x00336220 wrapper_cuMemcpyDtoA_v2_ptds wrapper
+0x00345130 wrapper_cuStreamWaitEvent_ptsz wrapper
+0x00368810 wrapper_cuSurfObjectDestroy wrapper
+0x0033e900 wrapper_cuMemAddressFree wrapper
+0x00354d30 wrapper_cuGraphKernelNodeCopyAttributes wrapper
+0x00356980 wrapper_cuGraphAddMemsetNode wrapper
+0x003730a0 wrapper_cuMemcpyDtoA wrapper
+0x00334720 wrapper_cuIpcOpenEventHandle wrapper
+0x00372ed0 wrapper_cuMemcpyDtoD wrapper
+0x0031dae0 wrapper_cuDeviceGetTexture1DLinearMaxWidth wrapper
+0x0033f800 wrapper_cuMemSetAccess wrapper
+0x0038a2e0 wrapper_cuEGLStreamConsumerReleaseFrame wrapper
+0x00370990 wrapper_cuStreamGetCaptureInfo_v2 wrapper
+0x00383890 wrapper_cuStreamWriteValue64_v2 wrapper
+0x00349830 wrapper_cuExternalMemoryGetMappedMipmappedArray wrapper
+0x00374120 wrapper_cuMemcpy2D wrapper
+0x00370bd0 wrapper_cuStreamGetCaptureInfo_v3 wrapper
+0x00388130 wrapper_cuMemBatchDecompressAsync wrapper
+0x0033d2d0 wrapper_cuStreamGetCtx_ptsz wrapper
+0x00372d00 wrapper_cuMemcpyDtoH wrapper
+0x003460d0 wrapper_cuStreamBeginCaptureToGraph_ptsz wrapper
+0x003618f0 wrapper_cuOccupancyMaxActiveBlocksPerMultiprocessorWithFlags wrapper
+0x00378550 wrapper_cuGraphicsResourceGetMappedPointer wrapper
+0x0034ab60 wrapper_cuStreamWriteValue32_v2_ptsz wrapper
+0x00363890 wrapper_cuTexRefSetMipmapFilterMode wrapper
+0x0034e0b0 wrapper_cuLaunchGrid wrapper
+0x00358ca0 wrapper_cuGraphAddExternalSemaphoresSignalNode wrapper
+0x0031df80 wrapper_cuDeviceGetProperties wrapper
+0x0037d080 wrapper_cuMemcpyAtoA_v2 wrapper
+0x003582b0 wrapper_cuGraphAddEmptyNode wrapper
+0x0038bf50 wrapper_cuGLRegisterBufferObject wrapper
+0x00357ad0 wrapper_cuGraphMemsetNodeSetParams wrapper
+0x00384360 wrapper_cuStreamBeginCapture wrapper
+0x00357800 wrapper_cuDeviceGetDevResource wrapper
+0x003760b0 wrapper_cuMemsetD32 wrapper
+0x00332f80 wrapper_cuDeviceRegisterAsyncNotification wrapper
+0x00392b60 wrapper_cuGLCtxCreate wrapper
+0x00380100 wrapper_cuLaunchHostFunc wrapper
+0x00365d30 wrapper_cuTexRefGetBorderColor wrapper
+0x0034b610 wrapper_cuFuncIsLoaded wrapper
+0x0037aa70 wrapper_cuStreamGetCaptureInfo wrapper
+0x003827a0 wrapper_cuStreamWaitValue64 wrapper
+0x0033fde0 wrapper_cuMemImportFromShareableHandle wrapper
+0x00367160 wrapper_cuTensorMapReplaceAddress wrapper
+0x0031c790 wrapper_cuDeviceGetExecAffinitySupport wrapper
+0x00380dd0 wrapper_cuEventRecord wrapper
+0x0033ee20 wrapper_cuMemRelease wrapper
+0x0037df50 wrapper_cuMemcpyDtoDAsync_v2 wrapper
+0x00366240 wrapper_cuTexRefGetAddressMode wrapper
+0x00351270 wrapper_cuGraphEventRecordNodeSetEvent wrapper
+0x0038d340 wrapper_cuGLSetBufferObjectMapFlags wrapper
+0x0036b6a0 wrapper_cuCoredumpSetAttribute wrapper
+0x00321500 wrapper_cuCtxDestroy_v2 wrapper
+0x00380840 wrapper_cuStreamQuery wrapper
+0x0034b890 wrapper_cuFuncLoad wrapper
+0x00380510 wrapper_cuStreamAttachMemAsync wrapper
+0x00373870 wrapper_cuMemcpyAtoA wrapper
+0x00335700 wrapper_cuMemHostUnregister wrapper
+0x0035a690 wrapper_cuGraphExecExternalSemaphoresSignalNodeSetParams wrapper
+0x00389da0 wrapper_cuEGLStreamProducerDisconnect wrapper
+0x003529e0 wrapper_cuGraphRemoveDependencies_v2 wrapper
+0x003527f0 wrapper_cuGraphRemoveDependencies wrapper
+0x00323790 wrapper_cuCtxSetLimit wrapper
+0x0036cad0 wrapper_cuGreenCtxWaitEvent wrapper
+0x00374460 wrapper_cuMemcpy3D wrapper
+0x00373290 wrapper_cuMemcpyAtoD wrapper
+0x0035da00 wrapper_cuGraphInstantiateWithParams_ptsz wrapper
+0x00377370 wrapper_cuMemsetD2D32_v2 wrapper
+0x00373670 wrapper_cuMemcpyAtoH wrapper
+0x00333720 wrapper_cuMemExportToShareableHandle wrapper
+0x003284c0 wrapper_cuKernelGetFunction wrapper
+0x0037ad00 wrapper_cuStreamGetCaptureInfo_ptsz wrapper
+0x0038a630 wrapper_cuEGLStreamProducerConnect wrapper
+0x0038a0f0 wrapper_cuEGLStreamConsumerAcquireFrame wrapper
+0x00382530 wrapper_cuStreamWriteValue64 wrapper
+0x0031fc50 wrapper_cuDevicePrimaryCtxRetain wrapper
+0x00367620 wrapper_cuTexRefDestroy wrapper
+0x00332da0 wrapper_cuMemAllocManaged wrapper
+0x00321df0 wrapper_cuCtxPopCurrent_v2 wrapper
+0x003418d0 wrapper_cuMemPoolSetAccess wrapper
+0x0037f830 wrapper_cuStreamWaitEvent wrapper
+0x0035ee80 wrapper_cuGraphLaunch_ptsz wrapper
+0x003539f0 wrapper_cuTexRefSetArray wrapper
+0x003929a0 wrapper_cuProfilerInitialize wrapper
+0x0034e290 wrapper_cuLaunchGridAsync wrapper
+0x0037bad0 wrapper_cuDevicePrimaryCtxRelease wrapper
+0x00337880 wrapper_cuMemcpyDtoHAsync_v2_ptsz wrapper
+0x0037f610 wrapper_cuMemcpy3DBatchAsync wrapper
+0x00383af0 wrapper_cuStreamWaitValue64_v2 wrapper
+0x0034bde0 wrapper_cuFuncSetCacheConfig wrapper
+0x00385e50 wrapper_cuGraphInstantiateWithParams wrapper
+0x00387660 wrapper_cuMemMapArrayAsync wrapper
+0x0034b3b0 wrapper_cuFuncGetModule wrapper
+0x003792f0 wrapper_cuGraphicsMapResources wrapper
+0x0038c5d0 wrapper_cuGLMapBufferObject_v2 wrapper
+0x003668e0 wrapper_cuTensorMapEncodeIm2col wrapper
+0x00349430 wrapper_cuExternalMemoryGetMappedBuffer wrapper
+0x00332be0 wrapper_cuMemHostGetFlags wrapper
+0x00336410 wrapper_cuMemcpyAtoD_v2_ptds wrapper
+0x0038b960 wrapper_cuGLGetDevices wrapper
+0x00328d40 wrapper_cuLibraryGetUnifiedFunction wrapper
+0x00386f40 wrapper_cuStreamSetAttribute wrapper
+0x0038c0f0 wrapper_cuGLMapBufferObject_v2_ptds wrapper
+0x0037fd10 wrapper_cuStreamAddCallback wrapper
+0x003564c0 wrapper_cuSurfRefGetArray wrapper
+0x0034e970 wrapper_cuGraphAddKernelNode_v2 wrapper
+0x003775a0 wrapper_cuArrayCreate wrapper
+0x0033cc10 wrapper_cuStreamGetDevice_ptsz wrapper
+0x003747f0 wrapper_cuMemcpyDtoHAsync wrapper
+0x0037a0d0 wrapper_cuStreamGetDevice wrapper
+0x003848a0 wrapper_cuStreamBeginCapture_v2 wrapper
+0x00351d60 wrapper_cuGraphBatchMemOpNodeGetParams wrapper
+0x003343c0 wrapper_cuIpcGetEventHandle wrapper
+0x0036c5e0 wrapper_cuDevResourceGenerateDesc wrapper
+0x00388a20 wrapper_cuCheckpointProcessGetState wrapper
+0x00393760 wrapper_cuGLMapBufferObject wrapper
+0x003383f0 wrapper_cuMemcpy3DPeerAsync_ptsz wrapper
+0x00350dd0 wrapper_cuGraphHostNodeSetParams wrapper
+0x00344f00 wrapper_cuStreamCreateWithPriority wrapper
+0x00344d00 wrapper_cuStreamCreate wrapper
+0x0033bf70 wrapper_cuArrayDestroy wrapper
+0x0035ad40 wrapper_cuGraphExecBatchMemOpNodeSetParams wrapper
+0x003799f0 wrapper_cuStreamGetPriority wrapper
+0x003385b0 wrapper_cuMemcpyBatchAsync_ptsz wrapper
+0x003432c0 wrapper_cuMulticastGetGranularity wrapper
+0x0035c8c0 wrapper_cuGraphNodeGetDependencies_v2 wrapper
+0x00339ef0 wrapper_cuMemsetD32_v2_ptds wrapper
+0x00320410 wrapper_cuDevicePrimaryCtxSetFlags_v2 wrapper
+0x003292b0 wrapper_cuKernelSetAttribute wrapper
+0x0037d690 wrapper_cuMemcpy2D_v2 wrapper
+0x00361ba0 wrapper_cuOccupancyMaxPotentialBlockSize wrapper
+0x00372680 wrapper_cuMemHostGetDevicePointer wrapper
+0x00364db0 wrapper_cuTexRefGetFilterMode wrapper
+0x00362fb0 wrapper_cuTexRefSetFormat wrapper
+0x0033ac20 wrapper_cuArrayGetDescriptor_v2 wrapper
+0x0031b430 wrapper_cuMemAllocPitch_v2 wrapper
+0x00323520 wrapper_cuCtxGetStreamPriorityRange wrapper
+0x0035bdd0 wrapper_cuGraphClone wrapper
+0x0031ecb0 wrapper_cuDeviceGetDefaultMemPool wrapper
+0x00359bd0 wrapper_cuUserObjectCreate wrapper
+0x00356750 wrapper_cuGraphMemcpyNodeSetParams wrapper
+0x0038d500 wrapper_cuMemPrefetchAsync_v2 wrapper
+0x0034a900 wrapper_cuStreamWaitValue64_v2_ptsz wrapper
+0x00342da0 wrapper_cuMulticastAddDevice wrapper
+0x0033c9d0 wrapper_cuStreamGetPriority_ptsz wrapper
+0x0035f970 wrapper_cuGraphKernelNodeGetAttribute wrapper
+0x0031b9b0 wrapper_cuDeviceGet wrapper
+0x00335e60 wrapper_cuMemcpyDtoH_v2_ptds wrapper
+0x00360650 wrapper_cuGraphRetainUserObject wrapper
+0x0031c2c0 wrapper_cuDeviceGetUuid_v2 wrapper
+0x0037ee60 wrapper_cuMemcpy3DPeerAsync wrapper
+0x00336f30 wrapper_cuMemcpy3D_v2_ptds wrapper
+0x00336bf0 wrapper_cuMemcpy2D_v2_ptds wrapper
+0x00321a60 wrapper_cuCtxPushCurrent_v2 wrapper
+0x0038b6d0 wrapper_cuGLGetDevices_v2 wrapper
+0x00337690 wrapper_cuMemcpyHtoDAsync_v2_ptsz wrapper
+0x0033f390 wrapper_cuMemMapArrayAsync_ptsz wrapper
+0x00347dc0 wrapper_cuEventCreate wrapper
+0x00351b50 wrapper_cuGraphExternalSemaphoresWaitNodeGetParams wrapper
+0x00322bb0 wrapper_cuModuleGetTexRef wrapper
+0x00374600 wrapper_cuMemcpyHtoDAsync wrapper
+0x00370550 wrapper_cuArray3DGetDescriptor wrapper
+0x00333560 wrapper_cuDeviceGetByPCIBusId wrapper
+0x0038af50 wrapper_cuGLInit wrapper
+0x00361f20 wrapper_cuOccupancyMaxPotentialBlockSizeWithFlags wrapper
+0x0034c1a0 wrapper_cuFuncSetSharedMemConfig wrapper
+0x00359f40 wrapper_cuGraphExecHostNodeSetParams wrapper
+0x0034efc0 wrapper_cuMemAdvise_v2 wrapper
+0x0031dd40 wrapper_cuDeviceGetAttribute wrapper
+0x00329e00 wrapper_cuMemGetAddressRange_v2 wrapper
+0x0032a3f0 wrapper_cuMemHostAlloc wrapper
+0x00383d50 wrapper_cuMemPrefetchAsync wrapper
+0x0033d7c0 wrapper_cuStreamIsCapturing_ptsz wrapper
+0x0031a630 wrapper_cuGetErrorName wrapper
+0x0036c340 wrapper_cuGreenCtxGetDevResource wrapper
+0x00327f30 wrapper_cuLibraryEnumerateKernels wrapper
+0x00347290 wrapper_cuStreamQuery_ptsz wrapper
+0x003561d0 wrapper_cuTexRefGetAddress_v2 wrapper
+0x00387e30 wrapper_cuMemAllocFromPoolAsync wrapper
+0x00346d30 wrapper_cuStreamGetCaptureInfo_v3_ptsz wrapper
+0x00326b60 wrapper_cuLinkDestroy wrapper
+0x0034d540 wrapper_cuParamSetf wrapper
+0x00324d10 wrapper_cuModuleLoad wrapper
+0x003707a0 wrapper_cuEventRecordWithFlags wrapper
+0x0034d2d0 wrapper_cuParamSeti wrapper
+0x003852f0 wrapper_cuStreamEndCapture wrapper
+0x003645e0 wrapper_cuTexRefSetFlags wrapper
+0x0036ff40 wrapper_cuMemAllocPitch wrapper
+0x00357470 wrapper_cuGraphGetRootNodes wrapper
+0x0033c270 wrapper_cuMipmappedArrayCreate wrapper
+0x00357100 wrapper_cuGraphGetNodes wrapper
+0x00347590 wrapper_cuStreamSynchronize_ptsz wrapper
+0x0033ec30 wrapper_cuMemCreate wrapper
+0x00328250 wrapper_cuLibraryGetModule wrapper
+0x00353630 wrapper_cuOccupancyMaxPotentialClusterSize wrapper
+0x00353200 wrapper_cuGraphAddNode_v2 wrapper
+0x00354190 wrapper_cuSurfObjectCreate wrapper
+0x0034d7b0 wrapper_cuParamSetv wrapper
+0x00349c80 wrapper_cuImportExternalSemaphore wrapper
+0x0033a780 wrapper_cuArrayCreate_v2 wrapper
+0x00345e10 wrapper_cuStreamBeginCapture_v2_ptsz wrapper
+0x0031e730 wrapper_cuDeviceSetMemPool wrapper
+0x0033bcb0 wrapper_cuMipmappedArrayGetSparseProperties wrapper
+0x00325a70 wrapper_cuModuleGetGlobal_v2 wrapper
+0x0034a6a0 wrapper_cuStreamWaitValue32_v2_ptsz wrapper
+0x00355920 wrapper_cuGraphNodeGetType wrapper
+0x0031e280 wrapper_cuDeviceComputeCapability wrapper
+0x003320e0 wrapper_cuEventRecordWithFlags_ptsz wrapper
+0x00337460 wrapper_cuMemcpyPeerAsync_ptsz wrapper
+0x003657d0 wrapper_cuTexRefGetMipmapLevelClamp wrapper
+0x0034eca0 wrapper_cuMemPrefetchAsync_v2_ptsz wrapper
+0x00360100 wrapper_cuUserObjectRelease wrapper
+0x0031cf20 wrapper_cuCtxGetApiVersion wrapper
+0x00353430 wrapper_cuOccupancyAvailableDynamicSMemPerBlock wrapper
+0x00347820 wrapper_cuStreamDestroy_v2 wrapper
+0x003595a0 wrapper_cuGraphAddBatchMemOpNode wrapper
+0x003635e0 wrapper_cuTexRefSetFilterMode wrapper
+0x0033a550 wrapper_cuMemsetD2D32_v2_ptds wrapper
+0x0038d1a0 wrapper_cuGLUnregisterBufferObject wrapper
+0x0036b8c0 wrapper_cuCoredumpSetAttributeGlobal wrapper
+0x003833d0 wrapper_cuStreamWriteValue32_v2 wrapper
+0x00351080 wrapper_cuGraphEventRecordNodeGetEvent wrapper
+0x00354a50 wrapper_cuGraphKernelNodeSetParams_v2 wrapper
+0x00376d10 wrapper_cuMemsetD32_v2 wrapper
+0x003391d0 wrapper_cuMemsetD32Async_ptsz wrapper
+0x0036a670 wrapper_cuGraphicsUnmapResources_ptsz wrapper
+0x00371060 wrapper_cuStreamUpdateCaptureDependencies_v2 wrapper
+0x0033ffc0 wrapper_cuMemRetainAllocationHandle wrapper
+0x00354350 wrapper_cuGraphicsUnregisterResource wrapper
+0x0035a450 wrapper_cuGraphExecEventWaitNodeSetEvent wrapper
+0x0035bb60 wrapper_cuDeviceSetGraphMemAttribute wrapper
+0x003239d0 wrapper_cuCtxGetLimit wrapper
+0x0037d280 wrapper_cuMemcpyHtoAAsync_v2 wrapper
+0x00340dc0 wrapper_cuMemPoolTrimTo wrapper
+0x00346af0 wrapper_cuStreamGetCaptureInfo_v2_ptsz wrapper
+0x00348b00 wrapper_cuEventElapsedTime wrapper
+0x00332730 wrapper_cuMemHostGetDevicePointer_v2 wrapper
+0x003228d0 wrapper_cuCtxSetFlags wrapper
+0x00382ef0 wrapper_cuStreamWriteValue64_ptsz wrapper
+0x00381460 wrapper_cuLaunchKernelEx wrapper
+0x0035c5b0 wrapper_cuGraphNodeGetDependencies wrapper
+0x0031d320 wrapper_cuDeviceTotalMem_v2 wrapper
+0x0036d360 wrapper_cuLinkCreate wrapper
+0x00345a00 wrapper_cuLaunchHostFunc_ptsz wrapper
+0x00324a60 wrapper_cuCtxWaitEvent wrapper
+0x00393e70 wrapper_cuProfilerStop wrapper
+0x0034bae0 wrapper_cuFuncSetAttribute wrapper
+0x00377a20 wrapper_cuTexRefSetAddress wrapper
+0x00371280 wrapper_cuTexRefGetAddress wrapper
+0x0031afa0 wrapper_cuKernelGetLibrary wrapper
+0x0031c060 wrapper_cuDeviceGetUuid wrapper
+0x003788f0 wrapper_cuCtxDestroy wrapper
+0x00381c50 wrapper_cuStreamBatchMemOp_ptsz wrapper
+0x00364870 wrapper_cuTexRefGetArray wrapper
+0x00386040 wrapper_cuGraphInstantiate wrapper
+0x0037e4c0 wrapper_cuMemcpy wrapper
+0x0036cd20 wrapper_cuGreenCtxStreamCreate wrapper
+0x0033d540 wrapper_cuStreamGetCtx_v2_ptsz wrapper
+0x003940a0 wrapper_cuVDPAUGetDevice wrapper
+0x00345610 wrapper_cuStreamAddCallback_ptsz wrapper
+0x00375a70 wrapper_cuMemsetD2D32Async wrapper
+0x0037ecc0 wrapper_cuMemcpy3DPeer wrapper
+0x00348040 wrapper_cuEventRecord_ptsz wrapper
+0x00351940 wrapper_cuGraphExternalSemaphoresSignalNodeGetParams wrapper
+0x0031f460 wrapper_cuCtxGetDevice wrapper
+0x00389a60 wrapper_cuEGLStreamConsumerDisconnect wrapper
+0x00347ab0 wrapper_cuStreamSetAttribute_ptsz wrapper
+0x00357fa0 wrapper_cuGraphAddChildGraphNode wrapper
+0x00392ea0 wrapper_cuVDPAUCtxCreate_v2 wrapper
+0x00366cf0 wrapper_cuTensorMapEncodeIm2colWide wrapper
+0x00351f70 wrapper_cuGraphMemAllocNodeGetParams wrapper
+0x003622a0 wrapper_cuTexRefSetAddress_v2 wrapper
+0x0033b2d0 wrapper_cuArrayGetPlane wrapper
+0x00378f70 wrapper_cuCtxPushCurrent wrapper
+0x00361390 wrapper_cuGraphConditionalHandleCreate wrapper
+0x00367fa0 wrapper_cuTexObjectGetResourceViewDesc wrapper
+0x0036c0d0 wrapper_cuCtxGetDevResource wrapper
+0x003862e0 wrapper_cuGraphInstantiate_v2 wrapper
+0x0037d9d0 wrapper_cuMemcpy3D_v2 wrapper
+0x00328770 wrapper_cuLibraryGetGlobal wrapper
+0x0037c050 wrapper_cuDevicePrimaryCtxSetFlags wrapper
+0x00365540 wrapper_cuTexRefGetMipmapLevelBias wrapper
+0x00349a10 wrapper_cuDestroyExternalMemory wrapper
+0x0031ca10 wrapper_cuDevicePrimaryCtxGetState wrapper
+0x00361640 wrapper_cuOccupancyMaxActiveBlocksPerMultiprocessor wrapper
+0x00341370 wrapper_cuMemPoolSetAttribute wrapper
+0x0033f180 wrapper_cuMemMap wrapper
+0x00383630 wrapper_cuStreamWaitValue32_v2 wrapper
+0x00329000 wrapper_cuKernelGetAttribute wrapper
+0x003370d0 wrapper_cuMemcpy3DPeer_ptds wrapper
+0x00387910 wrapper_cuMemFreeAsync wrapper
+0x003810f0 wrapper_cuLaunchKernel wrapper
+0x00336040 wrapper_cuMemcpyDtoD_v2_ptds wrapper
+0x0037c310 wrapper_cuMemcpyHtoD_v2 wrapper
+0x0038a920 wrapper_cuEGLStreamProducerPresentFrame wrapper
+0x00352ff0 wrapper_cuGraphAddNode wrapper
+0x00384600 wrapper_cuStreamBeginCapture_ptsz wrapper
+0x0033fb10 wrapper_cuMemGetAccess wrapper
+0x00338230 wrapper_cuMemcpy3DAsync_v2_ptsz wrapper
+0x00340310 wrapper_cuMemFreeAsync_ptsz wrapper
+0x00333d40 wrapper_cuMemGetAllocationPropertiesFromHandle wrapper
+0x0034df10 wrapper_cuLaunch wrapper
+0x00364080 wrapper_cuTexRefSetMaxAnisotropy wrapper
+0x0038bc10 wrapper_cuGLCtxCreate_v2 wrapper
+0x00331ec0 wrapper_cuStreamUpdateCaptureDependencies_v2_ptsz wrapper
+0x003442d0 wrapper_cuMemRangeGetAttribute wrapper
+0x00328a70 wrapper_cuKernelGetParamInfo wrapper
+0x003749e0 wrapper_cuMemcpyDtoDAsync wrapper
+0x0035a8c0 wrapper_cuGraphExecExternalSemaphoresWaitNodeSetParams wrapper
+0x003525e0 wrapper_cuGraphAddDependencies_v2 wrapper
+0x00389640 wrapper_cuEGLStreamConsumerConnect wrapper
+0x0037c4f0 wrapper_cuMemcpyDtoH_v2 wrapper
+0x0037d830 wrapper_cuMemcpy2DUnaligned_v2 wrapper
+0x0034c560 wrapper_cuLaunchKernel_ptsz wrapper
+0x00356e20 wrapper_cuGraphMemsetNodeGetParams wrapper
+0x0037f020 wrapper_cuMemcpyBatchAsync wrapper
+0x00386bf0 wrapper_cuGraphLaunch wrapper
+0x00393c40 wrapper_cuProfilerStart wrapper
+0x00373a70 wrapper_cuMemcpyHtoAAsync wrapper
+0x00348610 wrapper_cuEventSynchronize wrapper
+0x003892b0 wrapper_cuCheckpointProcessUnlock wrapper
+0x0037a7e0 wrapper_cuStreamIsCapturing wrapper
+0x00333a70 wrapper_cuMemGetAllocationGranularity wrapper
+0x003868a0 wrapper_cuGraphUpload wrapper
+0x00382c80 wrapper_cuStreamWaitValue32_ptsz wrapper
+0x003273c0 wrapper_cuLibraryUnload wrapper
+0x00378c00 wrapper_cuCtxPopCurrent wrapper
+0x00355670 wrapper_cuGraphNodeFindInClone wrapper
+0x00378250 wrapper_cuGraphicsResourceGetMappedEglFrame wrapper
+0x00376710 wrapper_cuMemsetD2D32 wrapper
+0x0037cc90 wrapper_cuMemcpyHtoA_v2 wrapper
+0x00325760 wrapper_cuModuleGetFunction wrapper
+0x003523f0 wrapper_cuGraphAddDependencies wrapper
+0x0037d480 wrapper_cuMemcpyAtoHAsync_v2 wrapper
+0x00352200 wrapper_cuGraphMemFreeNodeGetParams wrapper
+0x00385580 wrapper_cuGraphAddKernelNode wrapper
+0x003488b0 wrapper_cuEventDestroy_v2 wrapper
+0x0036dcc0 wrapper_cuDeviceTotalMem wrapper
+0x003201d0 wrapper_cuDevicePrimaryCtxReset_v2 wrapper
+0x0035a210 wrapper_cuGraphExecEventRecordNodeSetEvent wrapper
+0x0031ea00 wrapper_cuDeviceGetMemPool wrapper
+0x00352df0 wrapper_cuGraphExecMemsetNodeSetParams wrapper
+0x003423c0 wrapper_cuMemPoolImportFromShareableHandle wrapper
+0x00389460 wrapper_cuGraphicsEGLRegisterImage wrapper
+0x0033b9f0 wrapper_cuArrayGetSparseProperties wrapper
+0x003777d0 wrapper_cuArray3DCreate wrapper
+0x00387250 wrapper_cuIpcOpenMemHandle wrapper
+0x00340a90 wrapper_cuMemPoolGetAccess wrapper
+0x0031b7f0 wrapper_cuInit wrapper
+0x003720a0 wrapper_cuMemGetAddressRange wrapper
+0x00365fc0 wrapper_cuTexRefGetFlags wrapper
+0x0035c2f0 wrapper_cuGraphGetEdges_v2 wrapper
+0x0036af60 wrapper_cuCoredumpGetAttribute wrapper
+0x0033c450 wrapper_cuMipmappedArrayDestroy wrapper
+0x0037ea90 wrapper_cuMemcpyPeerAsync wrapper
+0x00322190 wrapper_cuCtxSetCurrent wrapper
+0x0037c6d0 wrapper_cuMemcpyDtoD_v2 wrapper
+0x0031f1f0 wrapper_cuCtxGetCurrent wrapper
+0x0036df20 wrapper_cuCtxCreate wrapper
+0x00324770 wrapper_cuCtxRecordEvent wrapper
+0x0034e730 wrapper_cuGraphCreate wrapper
+0x0037db70 wrapper_cuMemcpyHtoDAsync_v2 wrapper
+0x003593b0 wrapper_cuGraphExternalSemaphoresWaitNodeSetParams wrapper
+0x0033da50 wrapper_cuStreamCopyAttributes_ptsz wrapper
+0x00388860 wrapper_cuCheckpointProcessGetRestoreThreadId wrapper
+0x00334f30 wrapper_cuIpcOpenMemHandle_v2 wrapper
+0x00370e30 wrapper_cuGraphKernelNodeGetParams wrapper
+0x00329c60 wrapper_cuMemFree_v2 wrapper
+0x0033ce30 wrapper_cuStreamGetFlags_ptsz wrapper
+0x0031c560 wrapper_cuDeviceGetLuid wrapper
+0x003742c0 wrapper_cuMemcpy2DUnaligned wrapper
+0x0034f300 wrapper_cuMulticastBindMem wrapper
+0x0031a410 wrapper_cuGetErrorString wrapper
+0x0037bdb0 wrapper_cuDevicePrimaryCtxReset wrapper
+0x00343ee0 wrapper_cuMemAdvise wrapper
+0x00387b90 wrapper_cuMemAllocAsync wrapper
+0x0033dd70 wrapper_cuStreamGetAttribute_ptsz wrapper
+0x0031e4f0 wrapper_cuDeviceGetNvSciSyncAttributes wrapper
+0x003516d0 wrapper_cuGraphEventWaitNodeSetEvent wrapper
+0x00350bd0 wrapper_cuGraphHostNodeGetParams wrapper
+0x00325f60 wrapper_cuLinkCreate_v2 wrapper
+0x003673f0 wrapper_cuTexRefCreate wrapper
+0x00324ed0 wrapper_cuModuleLoadData wrapper
+0x00354730 wrapper_cuGraphKernelNodeGetParams_v2 wrapper
+0x00380b40 wrapper_cuStreamSynchronize wrapper
+0x0037b2b0 wrapper_cuStreamGetAttribute wrapper
+0x0034d080 wrapper_cuParamSetSize wrapper
+0x0033d080 wrapper_cuStreamGetId_ptsz wrapper
+0x0034a040 wrapper_cuWaitExternalSemaphoresAsync_ptsz wrapper
+0x003278e0 wrapper_cuLibraryGetManaged wrapper
+0x00335380 wrapper_cuIpcCloseMemHandle wrapper
+0x003652c0 wrapper_cuTexRefGetMipmapFilterMode wrapper
+0x0035d590 wrapper_cuGraphDestroyNode wrapper
+0x00341d90 wrapper_cuMemPoolDestroy wrapper
+#
+# --- internals verified during the 2026-09 decompilation (see docs/05) ---
+0x3a9c20 cudaHandlePoolAlloc verified
+0x3a2f50 cudaHandlePoolFree verified
+0x453ef0 cudaEngineContextRegisterHelper verified
+0x45a670 cudaDeviceInitEngineContexts verified
+0x4676f0 cudaEngineContextCreateHook verified
+0x481360 rmEngineContextAlloc verified
+0x453cc0 cudaEngineContextCleanup verified
diff --git a/userspace/cuda/570.144/annotations/subsystems.tsv b/userspace/cuda/570.144/annotations/subsystems.tsv
new file mode 100644
index 0000000..5a512bd
--- /dev/null
+++ b/userspace/cuda/570.144/annotations/subsystems.tsv
@@ -0,0 +1,37 @@
+# Open-IOV CUDA 570.144 subsystem index (tracked)
+#
+# Format: file_vaddr<TAB>name<TAB>subsystem<TAB>role<TAB>evidence
+# Addresses are FILE virtual addresses (libcuda+0x...). See README.md.
+#
+# subsystem values: api | engine | engine-engines | mem | stream | launch | sync |
+# module | rm | uvm | jit | table | unknown
+# evidence: decompiled (address inspected in the 570.144 corpus), trace (live),
+# relocation (derived from the stub), todo (open question)
+#
+# --- public API entry stubs (generated) ---
+0x310060 cuInit api exported entry stub; checks destroyed-state then jumps through interposition slot relocation
+0x310360 cuCtxCreate_v2 api exported entry stub relocation
+0x310b20 cuMemAlloc_v2 api exported entry stub relocation
+0x3106e0 cuModuleLoadData api exported entry stub relocation
+0x36f420 cuLaunchKernel api exported entry stub relocation
+0x36f3c0 cuStreamSynchronize api exported entry stub relocation
+# --- generated wrappers (tracing/tool dispatch) ---
+0x31b7f0 wrapper_cuInit api initial interposition target for cuInit relocation
+0x3206d0 wrapper_cuCtxCreate_v2 api initial interposition target for cuCtxCreate_v2 relocation
+0x329830 wrapper_cuMemAlloc_v2 api initial interposition target for cuMemAlloc_v2 relocation
+0x324ed0 wrapper_cuModuleLoadData api initial interposition target for cuModuleLoadData relocation
+0x3810f0 wrapper_cuLaunchKernel api initial interposition target for cuLaunchKernel relocation
+0x380b40 wrapper_cuStreamSynchronize api initial interposition target for cuStreamSynchronize relocation
+# --- engine/context bring-up (the cuCtxCreate path: crash solved, engine topology blocking; see docs/05) ---
+0x3a9c20 cudaHandlePoolAlloc engine bitmap handle allocator: lock, scan 64-bit words for first zero bit, return base + index*64 + bit decompiled
+0x3a2f50 cudaHandlePoolFree engine clears the handle bit under the pool mutex decompiled
+0x453ef0 cudaEngineContextRegisterHelper engine-engines per-engine registration: alloc handle, call create hook, call bind hook, publish engine id + descriptor into context arrays; called twice for engine index 0 (GR + secondary async CE) decompiled+trace
+0x45a670 cudaDeviceInitEngineContexts engine-engines walks 0x14-byte engine records (base+0x2fec for GR; +0x300c+(idx-1)*0x14; +0x350c; +0x351c+(idx-0x16)*0x14), checks engine existence via [table+0x4e00], calls the helper; sees only GR + CE0..4 because the GET_ENGINES_V2/classDB filter drops the async CE (see docs/05 section 3.6) decompiled+trace
+0x4676f0 cudaEngineContextCreateHook engine-engines hook at [table+0x40]+0x530; selects instance/class from the engine descriptor and calls rmEngineContextAlloc; its saved rbp was zeroed by the alloc reply's 16-byte class-params copy-back (crash solved, see docs/05 section 3.5) decompiled+trace
+0x481360 rmEngineContextAlloc rm builds NV_ESC_RM_ALLOC requests per class (0x80 device, 0x5/0x79 per-class table, 0x2080 subdevice array of 32, default generic) and returns small status codes; with a zeroed secondary engine record the class is rewritten to NV01_ROOT_CLIENT (0x41), status 0x19, and the context rolls back (rc=999) decompiled+trace
+0x453cc0 cudaEngineContextCleanup engine-engines failure-path cleanup of an engine context; runs on the rolled-back context (rc=999) decompiled
+# --- CURRENT BLOCKER (2026-09-23): engine list / classDB consistency (async CE COPY14) ---
+0x45a670 cudaDeviceInitEngineContexts engine-engines CURRENT BLOCKER: classDB-filtered engine list has 6 engines in the guest (GR + CE0..4) vs 7 on the host oracle (adds async CE COPY14: engDesc 0x793ceb0e, instance 14, client type 0x38, class 0xc9b5); without a classDB entry the walker reads a zeroed secondary record and the RM alloc is rejected (class 0x41, st 0x19). Record layout above; see docs/05 section 3.6 decompiled+trace
+# --- open questions ---
+0x4a7e90 FUN_004a7e90 unknown called by every generated wrapper; likely tool/trace dispatch or thread-data helper todo
+0x2cb940 FUN_002cb940 unknown large function (10 KB) reachable from the cuInit wrapper; candidate init implementation todo