runtime(cuda): Update cuda keywords, remove uncommonly used enumeration constants

closes: #14406

Signed-off-by: jiangyinzuo <jiangyinzuo@foxmail.com>
Signed-off-by: Christian Brabandt <cb@256bit.org>

diff --git a/runtime/syntax/cuda.vim b/runtime/syntax/cuda.vim
index 13d70e343abcbc1cf673dd7850022641f9b03e40..8306d096a023d73e5a9190619e626b1b858be6c4 100644 (file)
--- a/runtime/syntax/cuda.vim
+++ b/runtime/syntax/cuda.vim
@@ -1,7 +1,8 @@
 " Vim syntax file
 " Language:    CUDA (NVIDIA Compute Unified Device Architecture)
 " Maintainer:  Timothy B. Terriberry <tterribe@users.sourceforge.net>
-" Last Change: 2018 Feb 06
+" Last Change: 2024 Apr 04
+" Contributor:  jiangyinzuo
 
 " quit when a syntax file was already loaded
 if exists("b:current_syntax")
@@ -11,12 +12,13 @@ endif
 " Read the C++ syntax to start with
 runtime! syntax/cpp.vim
 
-" CUDA extentions
-syn keyword cudaStorageClass   __device__ __global__ __host__
-syn keyword cudaStorageClass   __constant__ __shared__
-syn keyword cudaStorageClass   __inline__ __align__ __thread__
+" CUDA extentions.
+" Reference: https://docs.nvidia.com/cuda/cuda-c-programming-guide/index.html#c-language-extensions
+syn keyword cudaStorageClass   __device__ __global__ __host__ __managed__
+syn keyword cudaStorageClass   __constant__ __grid_constant__ __shared__
+syn keyword cudaStorageClass   __inline__ __noinline__ __forceinline__ __inline_hint__
+syn keyword cudaStorageClass   __align__ __thread__ __restrict__
 "syn keyword cudaStorageClass  __import__ __export__ __location__
-syn keyword cudaStructure      template
 syn keyword cudaType           char1 char2 char3 char4
 syn keyword cudaType           uchar1 uchar2 uchar3 uchar4
 syn keyword cudaType           short1 short2 short3 short4
@@ -25,37 +27,23 @@ syn keyword cudaType                int1 int2 int3 int4
 syn keyword cudaType           uint1 uint2 uint3 uint4
 syn keyword cudaType           long1 long2 long3 long4
 syn keyword cudaType           ulong1 ulong2 ulong3 ulong4
+syn keyword cudaType           longlong1 longlong2 longlong3 longlong4
+syn keyword cudaType           ulonglong1 ulonglong2 ulonglong3 ulonglong4
 syn keyword cudaType           float1 float2 float3 float4
-syn keyword cudaType           ufloat1 ufloat2 ufloat3 ufloat4
+syn keyword cudaType           double1 double2 double3 double4
 syn keyword cudaType           dim3 texture textureReference
 syn keyword cudaType           cudaError_t cudaDeviceProp cudaMemcpyKind
 syn keyword cudaType           cudaArray cudaChannelFormatKind
 syn keyword cudaType           cudaChannelFormatDesc cudaTextureAddressMode
 syn keyword cudaType           cudaTextureFilterMode cudaTextureReadMode
-syn keyword cudaVariable       gridDim blockIdx blockDim threadIdx
+syn keyword cudaVariable       gridDim blockIdx blockDim threadIdx warpSize
+syn keyword cudaConstant       __CUDA_ARCH__
 syn keyword cudaConstant       __DEVICE_EMULATION__
+" There are too many CUDA enumeration constants. We only define a subset of commonly used constants.
+" Reference: https://docs.nvidia.com/cuda/cuda-runtime-api/group__CUDART__TYPES.html
 syn keyword cudaConstant       cudaSuccess
-" Many more errors are defined, but only these are listed in the maunal
-syn keyword cudaConstant       cudaErrorMemoryAllocation
-syn keyword cudaConstant       cudaErrorInvalidDevicePointer
-syn keyword cudaConstant       cudaErrorInvalidSymbol
-syn keyword cudaConstant       cudaErrorMixedDeviceExecution
-syn keyword cudaConstant       cudaMemcpyHostToHost
-syn keyword cudaConstant       cudaMemcpyHostToDevice
-syn keyword cudaConstant       cudaMemcpyDeviceToHost
-syn keyword cudaConstant       cudaMemcpyDeviceToDevice
-syn keyword cudaConstant       cudaReadModeElementType
-syn keyword cudaConstant       cudaReadModeNormalizedFloat
-syn keyword cudaConstant       cudaFilterModePoint
-syn keyword cudaConstant       cudaFilterModeLinear
-syn keyword cudaConstant       cudaAddressModeClamp
-syn keyword cudaConstant       cudaAddressModeWrap
-syn keyword cudaConstant       cudaChannelFormatKindSigned
-syn keyword cudaConstant       cudaChannelFormatKindUnsigned
-syn keyword cudaConstant       cudaChannelFormatKindFloat
 
 hi def link cudaStorageClass   StorageClass
-hi def link cudaStructure      Structure
 hi def link cudaType           Type
 hi def link cudaVariable       Identifier
 hi def link cudaConstant       Constant