blob: 8306d096a023d73e5a9190619e626b1b858be6c4 [file] [log] [blame]
Bram Moolenaar3577c6f2008-06-24 21:16:56 +00001" Vim syntax file
2" Language: CUDA (NVIDIA Compute Unified Device Architecture)
3" Maintainer: Timothy B. Terriberry <tterribe@users.sourceforge.net>
jiangyinzuoa2385c22024-04-08 22:48:43 +02004" Last Change: 2024 Apr 04
5" Contributor: jiangyinzuo
Bram Moolenaar3577c6f2008-06-24 21:16:56 +00006
Bram Moolenaar89bcfda2016-08-30 23:26:57 +02007" quit when a syntax file was already loaded
8if exists("b:current_syntax")
Bram Moolenaar3577c6f2008-06-24 21:16:56 +00009 finish
10endif
11
Bram Moolenaar72540672018-02-09 22:00:53 +010012" Read the C++ syntax to start with
13runtime! syntax/cpp.vim
Bram Moolenaar3577c6f2008-06-24 21:16:56 +000014
jiangyinzuoa2385c22024-04-08 22:48:43 +020015" CUDA extentions.
16" Reference: https://docs.nvidia.com/cuda/cuda-c-programming-guide/index.html#c-language-extensions
17syn keyword cudaStorageClass __device__ __global__ __host__ __managed__
18syn keyword cudaStorageClass __constant__ __grid_constant__ __shared__
19syn keyword cudaStorageClass __inline__ __noinline__ __forceinline__ __inline_hint__
20syn keyword cudaStorageClass __align__ __thread__ __restrict__
Bram Moolenaar3577c6f2008-06-24 21:16:56 +000021"syn keyword cudaStorageClass __import__ __export__ __location__
Bram Moolenaar3577c6f2008-06-24 21:16:56 +000022syn keyword cudaType char1 char2 char3 char4
23syn keyword cudaType uchar1 uchar2 uchar3 uchar4
24syn keyword cudaType short1 short2 short3 short4
25syn keyword cudaType ushort1 ushort2 ushort3 ushort4
26syn keyword cudaType int1 int2 int3 int4
27syn keyword cudaType uint1 uint2 uint3 uint4
28syn keyword cudaType long1 long2 long3 long4
29syn keyword cudaType ulong1 ulong2 ulong3 ulong4
jiangyinzuoa2385c22024-04-08 22:48:43 +020030syn keyword cudaType longlong1 longlong2 longlong3 longlong4
31syn keyword cudaType ulonglong1 ulonglong2 ulonglong3 ulonglong4
Bram Moolenaar3577c6f2008-06-24 21:16:56 +000032syn keyword cudaType float1 float2 float3 float4
jiangyinzuoa2385c22024-04-08 22:48:43 +020033syn keyword cudaType double1 double2 double3 double4
Bram Moolenaar3577c6f2008-06-24 21:16:56 +000034syn keyword cudaType dim3 texture textureReference
35syn keyword cudaType cudaError_t cudaDeviceProp cudaMemcpyKind
36syn keyword cudaType cudaArray cudaChannelFormatKind
37syn keyword cudaType cudaChannelFormatDesc cudaTextureAddressMode
38syn keyword cudaType cudaTextureFilterMode cudaTextureReadMode
jiangyinzuoa2385c22024-04-08 22:48:43 +020039syn keyword cudaVariable gridDim blockIdx blockDim threadIdx warpSize
40syn keyword cudaConstant __CUDA_ARCH__
Bram Moolenaar3577c6f2008-06-24 21:16:56 +000041syn keyword cudaConstant __DEVICE_EMULATION__
jiangyinzuoa2385c22024-04-08 22:48:43 +020042" There are too many CUDA enumeration constants. We only define a subset of commonly used constants.
43" Reference: https://docs.nvidia.com/cuda/cuda-runtime-api/group__CUDART__TYPES.html
Bram Moolenaar3577c6f2008-06-24 21:16:56 +000044syn keyword cudaConstant cudaSuccess
Bram Moolenaar3577c6f2008-06-24 21:16:56 +000045
46hi def link cudaStorageClass StorageClass
Bram Moolenaar3577c6f2008-06-24 21:16:56 +000047hi def link cudaType Type
48hi def link cudaVariable Identifier
49hi def link cudaConstant Constant
50
51let b:current_syntax = "cuda"
52
53" vim: ts=8