From: Thomas Schwinge Date: Fri, 29 Apr 2022 08:44:12 +0000 (+0200) Subject: 'include/cuda/cuda.h': Add parts necessary for nvptx-tools 'nvptx-run' X-Git-Tag: basepoints/gcc-14~6591 X-Git-Url: http://git.ipfire.org/cgi-bin/gitweb.cgi?a=commitdiff_plain;h=86f64400a5692499856d41462461327b93f82b8d;p=thirdparty%2Fgcc.git 'include/cuda/cuda.h': Add parts necessary for nvptx-tools 'nvptx-run' include/ * cuda/cuda.h (enum CUjit_option): Add 'CU_JIT_GENERATE_DEBUG_INFO', 'CU_JIT_GENERATE_LINE_INFO'. (enum CUlimit): Add 'CU_LIMIT_STACK_SIZE', 'CU_LIMIT_MALLOC_HEAP_SIZE'. (cuCtxSetLimit, cuGetErrorName): Add. --- diff --git a/include/cuda/cuda.h b/include/cuda/cuda.h index d7105fb331e..3938d05d150 100644 --- a/include/cuda/cuda.h +++ b/include/cuda/cuda.h @@ -97,7 +97,9 @@ typedef enum { CU_JIT_ERROR_LOG_BUFFER = 5, CU_JIT_ERROR_LOG_BUFFER_SIZE_BYTES = 6, CU_JIT_OPTIMIZATION_LEVEL = 7, - CU_JIT_LOG_VERBOSE = 12 + CU_JIT_GENERATE_DEBUG_INFO = 11, + CU_JIT_LOG_VERBOSE = 12, + CU_JIT_GENERATE_LINE_INFO = 13, } CUjit_option; typedef enum { @@ -117,6 +119,11 @@ enum { CU_STREAM_NON_BLOCKING = 1 }; +typedef enum { + CU_LIMIT_STACK_SIZE = 0x00, + CU_LIMIT_MALLOC_HEAP_SIZE = 0x02, +} CUlimit; + #define cuCtxCreate cuCtxCreate_v2 CUresult cuCtxCreate (CUcontext *, unsigned, CUdevice); #define cuCtxDestroy cuCtxDestroy_v2 @@ -128,6 +135,7 @@ CUresult cuCtxPopCurrent (CUcontext *); #define cuCtxPushCurrent cuCtxPushCurrent_v2 CUresult cuCtxPushCurrent (CUcontext); CUresult cuCtxSynchronize (void); +CUresult cuCtxSetLimit (CUlimit, size_t); CUresult cuDeviceGet (CUdevice *, int); #define cuDeviceTotalMem cuDeviceTotalMem_v2 CUresult cuDeviceTotalMem (size_t *, CUdevice); @@ -143,6 +151,7 @@ CUresult cuEventRecord (CUevent, CUstream); CUresult cuEventSynchronize (CUevent); CUresult cuFuncGetAttribute (int *, CUfunction_attribute, CUfunction); CUresult cuGetErrorString (CUresult, const char **); +CUresult cuGetErrorName (CUresult, const char **); CUresult cuInit (unsigned); CUresult cuDriverGetVersion (int *); CUresult cuLaunchKernel (CUfunction, unsigned, unsigned, unsigned, unsigned,