Coverage for cuda / bindings / cydriver.pyx: 66.02%

983 statements  

« prev     ^ index     » next       coverage.py v7.13.5, created at 2026-04-29 01:27 +0000

1# SPDX-FileCopyrightText: Copyright (c) 2021-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved. 

2# SPDX-License-Identifier: LicenseRef-NVIDIA-SOFTWARE-LICENSE 

3  

4# This code was automatically generated with version 13.2.0, generator version 0.3.1.dev1422+gf4812259e.d20260318. Do not modify it directly. 

5cimport cuda.bindings._bindings.cydriver as cydriver 

6  

7cdef CUresult cuGetErrorString(CUresult error, const char** pStr) except ?CUDA_ERROR_NOT_FOUND nogil: 

8 return cydriver._cuGetErrorString(error, pStr) 2DKhxEK

9  

10cdef CUresult cuGetErrorName(CUresult error, const char** pStr) except ?CUDA_ERROR_NOT_FOUND nogil: 

11 return cydriver._cuGetErrorName(error, pStr) 2rr[ksr]k^kDc_kDKhxEK/W'bghJp

12  

13cdef CUresult cuInit(unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

14 return cydriver._cuInit(Flags) 2a hhixtrjxkxlxmxnxoxpxqxrxsxtxuxvxwxxxyxzxAxBxCxurvrwrxryrzrArBrCrDrErKpFrGrHrIrJrKrLrMrNrOrPrQrRrSrTrUrDxExFxGxHxIxJxKxLxMxNxOxPxQxRxSxTxUx

15  

16cdef CUresult cuDriverGetVersion(int* driverVersion) except ?CUDA_ERROR_NOT_FOUND nogil: 

17 return cydriver._cuDriverGetVersion(driverVersion) 2a :W

18  

19cdef CUresult cuDeviceGet(CUdevice* device, int ordinal) except ?CUDA_ERROR_NOT_FOUND nogil: 

20 return cydriver._cuDeviceGet(device, ordinal) 2ixjxkxlxmxnxoxpxqxrxsxtxuxvxwxxxyxzxAxhxBxCxurvrwrxryrzrArBrCrDrErKpFrGrHrIrJrKrLrMrNrOrPrQrRrSrTrUrDxExFxGxHxIxJxKxLxMxNxOxPxQxRxSxTxUx

21  

22cdef CUresult cuDeviceGetCount(int* count) except ?CUDA_ERROR_NOT_FOUND nogil: 

23 return cydriver._cuDeviceGetCount(count) 2a FKGKHKIKJKKKLKMKNKOKPKQKRKSKTKUKVKWKXKYKZK0K1K2K3K4K5K6K7K8K9K!K#KVxWxXxYx;WZx0x1x2x`k!i{k3x#i|k}k4x5x6x7x8x$K9x!x#x$x%x'x(x)x*x+x,x-x.x/x:x;x=x?x@x[x]x^x_x`x{x|x}x~xaybycydyeyfygy~kal(b$i*d+d%iblcldlelbd,dihjhkhlhflglhlil)b'i-d.d(ijlklllmlcd/dmhnhohphnlolpl)iqlhy*irlsltl+iul,ivlwlxlyl*b-i:d;d.izlAlBlCldd=dqhrhshthDlElFlGl+b/i?d@d:iHlIlJlKled[duhvhwhxhLlMlNl,b;i]d^d=iOlPlQlRlfd_dyhzhAhBhSlTlUlVl-b?i`d{d@iWlXlYlZlgd|dChDhEhFh0l1l2l[i3l]i4l5l6l^i7l_i8l9l%K!l`i#l{i$l%l'K(K)K*K+K,K-K.K/K:K;K=K?K@K[K]K^K_K`K{K|K}K~KaLbLcLdLeLfLgLhLiLjLkLlLmLnLoLpLqLrLsLtLuLvLwLxLyLzLALBLCLDLELFLGLHLILJLKLLLMLNLOLPLQLRLSLTLiyjykylyLpmyny}doy~dpyY 'l(l)lqyrysyhd*ltyuyvywyxyyyzyAyByCyDyEyFyGyHyIyJyKyLyMyNyOyPyMp+lNp+f,lOp] ^ _ ` { | tr=WULVLWLXLYLQyVrWrXrYrZr0r1r2r3r4r5r6r7r8r9r!rEcZ FcZL0L1L2L3L4L5L6L7L8L9L!L#L$LGhae%LGcHcIcJc#r$r%r'r(r)r*r+r,r-r.r/r:r;r=r?r@r[r]r^r_r`r{r|r}r~rasbscsdsesfsgshs.b-l|iPpQpRpisjskslsmsnsospsqsrssstsusvswsxsyszsAsBsCsDsEsFsGsHsIsJsKsLsMsbeGbKc'LHhIhJh(L} id)L*LKh+Lce,Ljd/bLh,fMhdeNheeOh-Lfekd:bPh.Lge-f/LLc:L.f;L/f=L:f?L;f@L[LMc]L=fQhheld;bRh^LShTh_LieUhjeVh`Lke{Lmd|L=bWh}Lle~L?f@fXhndaMNcbMme}iRyYhcMHbdMIbne.leMZhfM0hgMSp?WhMiM/ljM:l;l=lK kM?lghlMmMnMoMpMqMrMsMtMuM@l[l]lNsOsPsQsRsSs^l_l`l{l|l}l~lambmcmdmemfmgmhmimjmkmlmmmnmompmqmrmsmtmumvmwmxmymzmAmBmCmDmEmFmGmHmImJmKmLmMmNmOmPmQmRmSmTmUmVmWmXmYmZm0m1m2m3m4mTs5m6m7m8m~i?bTpvMwMajSybjcjdjTy9m!m#moepe1hUpUyUs$m%mej'mVs(mfj@bVpxMVygjWyhjijjjXy)m*m+m,mqere2hWpYyWs-m.mJbsetekj[f]f^fodue3h_f`fve9 wepdOcPcqd4hrdsdtdxeKb5hLbQc{f6hudvd~ abMb) * + , 7hbb|f}f~fag8h/m:mRcwdbgXp;m=m?mlj[bYpmjnjojpjZy@m[m]m^myeyMze9hZp0y_m`mqj!hNb{m1y#hXs$h%h'hYsrjsjtjujxd2yydcg|mZs0pvjwjxjcbzdAd(hAeBeCeScDedgEeFeyj)hOb}m3y*hzjAj+h0sBjCjDjEjBd4yCdeg~m1sFjGj,h-hGeHeIeJe.hKeLeMeNedbDdEdOePeQeFdfgReSean]b1pHjIjJjKjbncndnTeUe/h5yenfngghgigjggnhninjnkn:h^bkglgGdHdmgLjVeWeXeYeTcZeMj0e1e_bUcVcWcId`b{beb|b}b~blnacNjOjPjQj6ymnnnonpn2e3e;h2p7yqnrn0 PbQbbcXcYcZc0c- 1c2cJd4e5eKd6e7eRjcc=h?h8e9e@hsnngogpgtn!eLdqgunrgsgvndcSjTjUjVjwnxnyn#e$e[hznAn]htgfbWj2sug3pvgwgxg4p^h_h`h{h3c3s4c%eXj5p|h}hBnCnYjec6pzMAMZj8y0j1j2j9yDnEnFnGn'e(e~h7p!y4sHnInRb)e*e3jygzgAgMd+eaiBgCg,e! -eNd5c6cOdbiPdQdRd.eSb4jTb7ccidiSdTdgbhbUb. / : ; ibDgEgFgGgeiJnKn8cUdHg8pLnMnNn5jfc9p6j7j8j9j#yOnPnQnRn/eBM:efi5s$ySnTnUn!jgc!pCM#j%y$j%j'j'yVnWnXnYn;eDM=egi6s(y7sZn0n(jjbVdWdhi?e@e[e9c]eIg^e_e)jiiVb1n)yji*j+jki8s,j-j.j/jXd*yYdJg#p9s:j;jlimi`e{e|e}eni~eafbfcfkbZd0ddfefff1dKggfhf2nhc$p=j?j@j[j3n4n5nifjfoi+y6n7nLgMgNgOg8n9n!n#n$npiicPgQg2d3dRg]jkflfmfnf!cof^jpfqfjc#c$c%c4dkclclbmcncoc%npc%p_j`j{j|j,y'n(n)n*nrfsfqi!s-y+n,n1 WbXbqc'c(c)c*c= +c,c5dtfuf6dvfwf-nrc}j~jSgTgak'prisiti.nxfyfui(pviwi/nscbkckdkek:n;n=nzfAfxi?n@nyiUgmbfk#sVgWgXgYg)pziAiBiCi-c$s.cBf[n*pDiEi]nEMFM/c:c7d8d%s's^ngktc+pGM.yhk/yikjkkk:y_n`n{n|nCfDfFi,p-pHM(s)sIM;y.p}n~naolkuc/pJMKMmk=ynkokpk?ybocodoeoEfFfGi:p@y*sfogohoqkvc;pLM[yrk]ysktkuk^yiojokoloGfHfHi=p_y+smonooovkwc?pMM`ywk{yxkykzk|ypoqorosoIfJfIi@p}y,stouovoAkxc[pNM~yBkazCkDkEkbzwoxoyozoKfLfJi]pcz-sAoBoCoFkyc^pOMdzGkezHkIkJkfzDoEoFoGoMfNfKi_pgz.sHoIoJoKkzc`pPMQMLkhzMkNkOkizKoLoMoNoOfPfLi/s:sjz;sOoPoQoPkAc{pRMSMQkkzRkSkTklzRoSoToUoQfRfMi=s?smz@sVoWoTMUM[sVMWMXMYMZM0M1M2M3M4M5M6M7M8M9M!M#M$M%M'M(M)M*M+M,M-M.M/M:M;M=M?M@M[M]M^M_M]s^s`M{M|M}M~MaNbNcNdNeNfNgN_s`s{s|s}s~shNiNjNkNlNmNnN|poNpNqNrNsNtNuNvNwNxNyNzNANBNCNDNENFNGNHNINJNKNLNMNatbtctdtetftgthtitjtktltmtntotptqtrtstttutvtwtxtytztAtBtCtDtEtFtGtHtItJtKtLtNNONPNMtNtOtQNRNSNTNUNVNWNXNYNZN0N1N2N3N4N5N6N7N8NSfTfUfVfWfXfYfZf0f1f2f3f4f5f6f7f8f9f!f#f$f9N!N#N$N%N'N(N)N*N+N,N-N.N/N:N;N=N?N@N[N

24  

25cdef CUresult cuDeviceGetName(char* name, int length, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

26 return cydriver._cuDeviceGetName(name, length, dev) 2TL@WXoYoLpPt}d~dY # UkVkWkXkYkZk0k1k(l}pMpQtRtStNpTt+fNiZg0g%f'fOiPiUtVtOpWttr[W]Nnz.y

27  

28cdef CUresult cuDeviceGetUuid(CUuuid* uuid, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

29 return cydriver._cuDeviceGetUuid_v2(uuid, dev) 2Zo'l)l*l+l,lhh]W^W_W`W{Wozpzce/b,fdeeefe:bgehe;biejeke=ble?fIbZh0hTsVyqj!hNb{m1y#hXs$h%h'hYsrjsjtjujxd2yydcg|mZs0pvjwj/c:c7d8d[y`y~ydz

30  

31cdef CUresult cuDeviceGetLuid(char* luid, unsigned int* deviceNodeMask, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

32 return cydriver._cuDeviceGetLuid(luid, deviceNodeMask, dev) 

33  

34cdef CUresult cuDeviceTotalMem(size_t* numbytes, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

35 return cydriver._cuDeviceTotalMem_v2(numbytes, dev) 

36  

37cdef CUresult cuDeviceGetTexture1DLinearMaxWidth(size_t* maxWidthInElements, CUarray_format pformat, unsigned numChannels, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

38 return cydriver._cuDeviceGetTexture1DLinearMaxWidth(maxWidthInElements, pformat, numChannels, dev) 

39  

40cdef CUresult cuDeviceGetAttribute(int* pi, CUdevice_attribute attrib, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

41 return cydriver._cuDeviceGetAttribute(pi, attrib, dev) 2a ^NR S 2 W $ nbc d e f g h i j k l m n o p q r s t u G H I J qzrz~prrXtszYt`k!i{k#i|k}kaq;c=c?c9dX |W}WobpbqbYbrb3 4 5 % Zb0b1bBc~WbqcqdqeqfqgqQi2k~kal(b$i*d+d%ibd,dihjhkhlhhlil)b'i-d.d(icd/dmhnhohphpl)iql*irlsltl+iul,ivlwlxlyl*b-i:d;d.idd=dqhrhshthFlGl+b/i?d@d:ied[duhvhwhxhMlNl,b;i]d^d=ifd_dyhzhAhBhUlVl-b?i`d{d@igd|dChDhEhFh2l[i3l]i4l5l6l^i7l_i8l9l!l`i#l{i$l%laX3khq!dbX@ccX_N`N{N|N}N~Nsbtbubvb2b#d$diq(fT ? @ 3bM L z A B b ' C U V wb4b5b[c6bN ZoY 'l# jq)lkq*llq+lmq,lnqhhtr0otzuz1g2gVrvzwzxzyzzzAzBzCzDzWrEzFzGzHzIzJzKzLzMzNzOzPzXrQzRzSzTzUzVzWzXzYrYzZz0z1z2z3z4z5z6z7z8z9z!z#z$z%z'z(z)z*z+z,z-z.z/z:z;z=z?z@z[zZr0r]z^z_z`z{z|z}z~zaAbAcAdAeAfAgAhA1riAjAkAlAmAnAoApAqArAsA2rtAuAvAwAxAyAzAAA3rBACA4rDAEAFAGAHA5r6rIAJAKALA7rMANAOAPAQARASATAUA8rVAWAXA9rYAZA0A1A!r2A3A4A5AZ xbCcyb%d'dRiSiTi)fUiVi(daOGcHcIcJc#r$r%r'r(r)r*r+r,r-r.r/r:r;r=r?r@r[r]r^r_r`r{r|r}r~rasbscsdsesfsgshs6AWiXibeGb4kKc5kZtHhIhJh0t} Yiid6kKhcejd/bLhMhdeNheeOhfekd:bPhge-f7ALc8A.f9A/f!A:f#A;f$AMc%A=f'AQhheld;bRhThieUhjeVhkemd=bWhle?f@fXhndNcRy3gZi7kHbIbne.lZh0hbO]c^c'b_cSpcOoq/lpq:l;l=lK ?lghqqrqsqtquqvqwqxqyqzq@l[l]lNsOsPsQsRsSs(A^l)A_l*A`l+A{l,A|l-A}l1t~l2tam3tbm4tcm5tdm6tem7tfm8tgm9thm!tim#tjm$tkm%tlm'tmm(tnm)tom*tpm+tqmrmsm.Atm/Aum:Avm;Awm=Axm?Aym@Azm[AAm]ABm^ACm_A`ADm{AEm|AFm}AGm~AHmaBImbBJmcBKmdBLmeBMmNmOmPmQmRmSmTmUmAqVmWmXmYmZm0m1m2m3mTs8m~i?bajdj#moepe1hUpej'm(mfj@bgjjj,mqere2hWpJbsetekj[f]f^fodue3h_f`fve9 wepdOcPcqd4hrdsdtdxeKb5hLbQc{f6hudvd~ abMb) * + , 7hbb|fagRcwdbg?mlj[bmjpj^myeze9hZpqj!hNb#h'hujxdydcg|mxjcbzdAd(hAeBeCeScDedgEeFeyj)hOb*h+hEjBdCdeg~mdbDdEdOePeQeFdfgReSean]bHjKjTeUe/h:h^bkglgGdHdmgLjVeWeXeYeTcZeMj0e1e_bUcVcWcId`b{beb|b}b~blnacNjQjpn2e3e;h2p0 PbQbbcXcYcZc0c- 1c2cJd4e5eKd6e7eRjcc=h?h8e9e@hsnngogpgtn!eLdqgunrgsgvndcSjVj#e$e[h]htgfbugxg{h3c4c%eXjCnYjecZj2jGn'e(e~h7pRb)e*e3jygzgAgMd+eaiBgCg,e! -eNd5c6cOdbiPdQdRd.eSb4jTb7ccidiSdTdgbhbUb. / : ; ibDgGg8cUdHgNn5jfc6j9jRn/e:efi5sUn!jgc#j'jYn;e=egi6s(jjbVdWdhi?e@e[e9c]eIg^e_e)jiiVbjiki/jXdYdJg#pkbZd0ddfefff1dKggfhf2nhc=j[jifjfoipiicPgQg2d3dRg]jkflfmfnf!cof^jpfqfjc#c$c%c4dkclclbmcncoc%npc_j|j*nrfsfqi!s1 WbXbqc'c(c)c*c= +c,c5dtfuf6dvfwf-nrc}j~jSgTgak'prisiti.nxfyfui(pviwi/nscbkekzfAfxiyiUgmbVgYgCi-c.cBf[n/c:c7d8d%s's^ngktchkkk|nCfDfFi,p-p(s)saolkucmkpkeoEfFfGi:phoqkvcrkukloGfHfHi=poovkwcwkzksoIfJfIi@pvoAkxcBkEkzoKfLfJi]pCoFkycGkJkGoMfNfKi_pJoKkzcLkOkNoOfPfLi/s:sQoPkAcQkTkUoQfRfMi=s?sdOeO[sfOgOhOiO]s^s_s`s{s|s}s~s|patbtctdtetftgthtitjtktltmtntotptqtrtstttutvtwtxtytztAtBtCtDtEtFtGtHtItJtKtLtMtNtOtSfTfUfVfWfXfYfZf0f1f2f3f4f5f6f7f8f9f!f#f$f1o

42  

43cdef CUresult cuDeviceGetHostAtomicCapabilities(unsigned int* capabilities, const CUatomicOperation* operations, unsigned int count, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

44 return cydriver._cuDeviceGetHostAtomicCapabilities(capabilities, operations, count, dev) 

45  

46cdef CUresult cuDeviceGetNvSciSyncAttributes(void* nvSciSyncAttrList, CUdevice dev, int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

47 return cydriver._cuDeviceGetNvSciSyncAttributes(nvSciSyncAttrList, dev, flags) 

48  

49cdef CUresult cuDeviceSetMemPool(CUdevice dev, CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil: 

50 return cydriver._cuDeviceSetMemPool(dev, pool) 2jO

51  

52cdef CUresult cuDeviceGetMemPool(CUmemoryPool* pool, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

53 return cydriver._cuDeviceGetMemPool(pool, dev) 27b8b9bw ( x y D ' E F 1g2gWiXi8kbeYi3gK ~iejfjve9 wepdOcPcqd4hrdsdtdxeKb5hLbQc{f6hudvdlj!h)htgYj,e! -eNd5c6cOdbiPdQdRd.eSb4jTb7ccidiSdTd5j!jiiUggklkqkvkAkFkKkPkSfTfUfVfWfXfYfZf0f1f2f3f4f5f6f7f8f9f!f#f$f1o

54  

55cdef CUresult cuDeviceGetDefaultMemPool(CUmemoryPool* pool_out, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

56 return cydriver._cuDeviceGetDefaultMemPool(pool_out, dev) 2jO

57  

58cdef CUresult cuDeviceGetExecAffinitySupport(int* pi, CUexecAffinityType typename, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

59 return cydriver._cuDeviceGetExecAffinitySupport(pi, typename, dev) 

60  

61cdef CUresult cuFlushGPUDirectRDMAWrites(CUflushGPUDirectRDMAWritesTarget target, CUflushGPUDirectRDMAWritesScope scope) except ?CUDA_ERROR_NOT_FOUND nogil: 

62 return cydriver._cuFlushGPUDirectRDMAWrites(target, scope) 

63  

64cdef CUresult cuDeviceGetProperties(CUdevprop* prop, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

65 return cydriver._cuDeviceGetProperties(prop, dev) 

66  

67cdef CUresult cuDeviceComputeCapability(int* major, int* minor, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

68 return cydriver._cuDeviceComputeCapability(major, minor, dev) 

69  

70cdef CUresult cuDevicePrimaryCtxRetain(CUcontext* pctx, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

71 return cydriver._cuDevicePrimaryCtxRetain(pctx, dev) 2hhurvrwrxryrzrArBrCrDrErKpFrGrHrIrJrKrLrMrNrOrPrQrRrSrTrUr

72  

73cdef CUresult cuDevicePrimaryCtxRelease(CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

74 return cydriver._cuDevicePrimaryCtxRelease_v2(dev) 2dXeXfXgXhXiXjXkXlXmXnXKpoXpXqXrXsXtXuXvXwXxXyXzXAXBXCXDXEX

75  

76cdef CUresult cuDevicePrimaryCtxSetFlags(CUdevice dev, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

77 return cydriver._cuDevicePrimaryCtxSetFlags_v2(dev, flags) 

78  

79cdef CUresult cuDevicePrimaryCtxGetState(CUdevice dev, unsigned int* flags, int* active) except ?CUDA_ERROR_NOT_FOUND nogil: 

80 return cydriver._cuDevicePrimaryCtxGetState(dev, flags, active) 

81  

82cdef CUresult cuDevicePrimaryCtxReset(CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

83 return cydriver._cuDevicePrimaryCtxReset_v2(dev) 

84  

85cdef CUresult cuCtxCreate(CUcontext* pctx, CUctxCreateParams* ctxCreateParams, unsigned int flags, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

86 return cydriver._cuCtxCreate_v4(pctx, ctxCreateParams, flags, dev) 2ixjxkxlxmxnxoxpxqxrxsxtxuxvxwxxxyxzxAxBxCxDxExFxGxHxIxJxKxLxMxNxOxPxQxRxSxTxUx

87  

88cdef CUresult cuCtxDestroy(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

89 return cydriver._cuCtxDestroy_v2(ctx) 2FXGXHXIXJXKXLXMXNXOXPXQXRXSXTXUXVXWXXXYXZX0X1X2X3X4X5X6X7X8X9X!X#X$X%X'X(X)X*X+X

90  

91cdef CUresult cuCtxPushCurrent(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

92 return cydriver._cuCtxPushCurrent_v2(ctx) 20i

93  

94cdef CUresult cuCtxPopCurrent(CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

95 return cydriver._cuCtxPopCurrent_v2(pctx) 2kOlOmOnOoOpOqOrOsOtOuOvOwOxOyOzOAOBOCODOEOFOGOHOIOJOKOLOMONOOOPOQOROfBgBhBiBjBkBlBmBnBoBpBqBrBsBtBuBvBwBxByBzBSOABBBCBDBEB,tFBGBTOUOHBIBJBKBLBMBNBOBPBQBRBSBTBVOUBVBWBXBYBZB0B1B2B3B4B5B6B7BWO-t.t8B9BXO!B#B$B%B'B(B)B*B+B,B-B.B/BYO/t:t:B;BZO0O1O=B?B@B[B]B^B2O3O_B`B{B|B}B~BaCbCcCdCeCfCgChCiCjCkC;t=tlCmCnCoCpCqCrCsCtCuCvCwCxCyCzCACBC?t@tCCDCECFCGCHCICJCKCLCMCNCOCPCQCRCSC[t]tTCUCVCWCXCYCZC0C1C2C3C4C5C6C7C8C9C^t_t!C#C$C%C'C(C)C*C+C,C-C.C/C:C;C=C?C@C[C]C^C_C`C{C|C4O}C~CaDbDcDdD5O6O7O8O9O!O#O$O%O'O(O)O*O+O,O-O.O/O:O;O=O?O@O[O]O^O_O`O{O|O}O~OaPbPcPdPePfPgPhPiPjPkPlPmPnPoPpPqPrPsPtPuPvPwPxPyPzPAPBPCPDPEPFPGPHPIPJPKPLPMPNPOPPPQPRPSPTPUPVPWPXPYPZP0P1P2P3P4P5P6P7P8P9P!P#P$P%P'P(P)P*P+P,P-P.P/P:P;P=P?P@P[P]P^P_P`P{P|P}P~PaQbQcQdQeQfQgQhQiQjQkQlQmQnQoQpQqQrQsQtQuQvQwQxQyQzQAQBQCQDQEQFQGQHQIQJQKQLQMQNQOQPQQQRQSQTQUQVQWQXQYQZQ0Q1Q2Q3Q4Q5Q6Q7Q8Q9Q!Q#Q$Q%Q'Q(Q)Q*Q+Q,Q-Q.Q/Q:Q;Q=Q?Q@Q[Q]Q^Q_Q`Q{Q|Q}Q~QaRbRcRdReRfRgRhRiRjRkRlRmRnRoRpRqRrRsRtRuRvRwRxRyRzRARBRCRDRERFRGRHRIRJRKRLRMRNRORPRQRRRSRTRURVRWRXRYRZR0R1R2R3R4R5R6R7R8R9R!R#R$R%R'R(R)R*R+R,R-R.R/R:R;R=R?R@R[R]R^R_R`R{R|R}R~RaSbScSdSeSfSgShSiSjSkSlSmSnSoSpSqSrSeDfDgDhDsStSiDjD`t{tkDlDmDnDoDuSpDqDrDvSsDtDuDvDwDwSxDyDzDADBDxSySCDDD|t}tEDFDGDHDIDzSJDKDLDASMDNDODPDQD~tauRDSDTDUDVDWDXDYDZDbucudueuBqCqfuguhuiuju0Dku1Dlumu2Dnuoupuquru3D4D5D6D7D8D9D!Dsutu#D$D%D'D(D)D*D+D,D-D.D/D:D;D=Duuvu?D@D[D]D^DBS_DCS`D{DDS|D}D~DaEbEcEdEESeEfEwuxugEhEiEjEkEFSlEGSmEnEHSoEpEqErEsEtEyuzuuEvEwExEyEzEAEBECEAuBuCuDuDEEuFuGuHuIuJuKuLuEEMuFENuOuGEPuQuRuSuTuUuVuWuXuYuZu0u1u2uHE3u4uIEJEKELEMENEOEPEQERESE5u6uTEUEVEWEXEYEZE0E1E2E3E4E5E6E7E8E9E!E#E$E%E'E(E7u8u)E*E+E,E-E.E/E:E;E=E?E@E9u!u[E]E^E_E`E{E|E}E~EaFbFcF#u$udFeFfFgFhFISiFjFkFJSlFmFnFoF%u'upFqFrFsFtFuF(u)uvFwFxFyFzFAFBFCFDFEF*u+uFFGFHFIFJFKSKFLFMFNFOFPFQFRFSF,u-uTFUFVFWFXFYFZF0F1F.u/u:u;u2F=u?uDqEq@u[u]u^u_u3F`u4F{u|u5F}u~uav6F7F8F9F!FLSMS#F$Fbvcv%F'F(F)F*FNS+F,F-FOS.F/F:F;F=Fdvev?F@F[F]F^F_F`F{F|FfvgvhvivFqGqjvkvlvmvnv}Fov~FpvqvaGrvsvtvuvvvbGcGdGeGfGgGhGiGwvxvjGkGlGmGnGoGpGqGrGsGtGuGvGwGxGyvzvyGzGAGBGCGPSDGQSEGFGRSGGHGIGJGKGLGMGSSNGOGAvBvPGQGRGSGTGTSUGUSVGWGVSXGYGZG0G1G2GCvDv3G4G5G6G7G8G9G!G#GEvFvGvHv$GIvJvKvLvMvNvOvPv%GQv'GRvSv(GTvUvVvWvXvYvZv0v1v2v3v4v5v6v)G7v8v*G+G,G-G.G/G:G;G=G?G@G9v!v[G]G^G_G`G{G|G}G~GaHbHcHdHeHfHgHhHiHjHkHlHmHnH#v$voHpHqHrHsHtHuHvHwHxHyHzH%v'vAHBHCHDHEHFHGHHHIHJHKHLH(v)vMHNHOHPHQHWSRHSHTHXSUHVHWHXH*v+vYHZH0H1H2H3H,v-v4H5H6H7H8H9H!H#H$H%H.v/v'H(H)H*H+HYS,H-H.H/H:H;H=H?H@H:v;v[H]H^H_H`H{H|H}H~H=v?v@v[vaI]v^vHqIq_v`v{v|v}vbI~vcIawbwdIcwdweweIZS0S1S2SfIgIhIiI3S4SjIkIfwgwlImInIoIpI5SqIrIsI6S7S8S9S!S#StIuIvIwIxIyIzIAI$S%SBICIhwiwDIEIFIGIHI'SIIJIKI(SLIMINIOIPIQIRISI)S*STIUIjwkwVIWIXIYIZI+S0I1I2I,S3I4I5I6I7I8I9I!I-S.S#I$Ilwmw%I'I(I)I*I/S+I,I-I:S.I/I:I;I=I?I@I[I;S=S]I^Inwow_I`I{I|I}I?S~IaJbJ@ScJdJeJfJgJhJiJjJ[S]SkJlJpwqwmJnJoJpJqJ^SrJsJtJ_SuJvJwJxJyJzJAJBJ`S{SCJDJrwswEJFJGJHJIJ|SJJKJLJ}S~SMJNJOJPJQJRJSJTJaTbTUJVJtwuwWJXJYJZJ0JcT1J2J3JdTeT4J5J6J7JfTgThTiTjTkTlTmTnToTpTqTrTsTtTuTvTwTxTyTzTATBTCTDTETFTGTHTITJTKTLTMTNTOTPTQTRTSTTTUTVTWTXTYTZT0T1T2T3T4T5T6T7T8T9T!T#T$T%T'T(T)T*T+T,T-T.T/T:T;T=T?T@T[T0i]T^T_T`T{T|T}T~TaUbUcUdUeUfUgUhUiUjUkUlUmUnUoUpUqUrUsUtUuUvUwUxUyUzUAUBUCUDUEUFUGUHUIUJUKULUMUNUOUPUQURUSUTUUUVUWUXUYUZU0U1U2U3U4U5U6U7U8U9U!U#U$U%U'U(U)U*U+U,U-U.U/U:U;U=U?U@U[U]U^U_U`U{U|U}U~UaVbVcVdVeVfVgVhViVjVkVlVmVnVoVpVqVrVsVtVuVvVwVxV

96  

97cdef CUresult cuCtxSetCurrent(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

98 return cydriver._cuCtxSetCurrent(ctx) 2FKGKHKIKJKKKLKMKNKOKPKQKRKSKTKUKVKWKXKYKZK0K1K2K3K,X4K5K6K7K8K9K!K#KVxWxXxYxZx0xyV1x2x`k!i{k3x#i|k}k4x5x6x7x8x$K9x!x#x$x%x'x(x)x*x+x,x-x.x/x:x;x=x?x@x[x]x^x_x`x{x|x}x~xaybycydyeyfygy~kal(b$i*d+d%iblcldlelbd,dihjhkhlhflglhlil)b'i-d.d(ijlklllmlcd/dmhnhohphnlolpl)iqlhy*irlsltl+iul,ivlwlxlyl*b-i:d;d.izlAlBlCldd=dqhrhshthDlElFlGl+b/i?d@d:iHlIlJlKled[duhvhwhxhJqLlMlNl,b;i]d^d=iOlPlQlRlfd_dyhzhAhBhSlTlUlVl-b?i`d{d@iWlXlYlZlgd|dChDhEhFh0l1l2l[i3l]i4l5l6l^i7l_i8l9l%K!l`i#l{i$l%l'K(K)K*K+K,K-K.K/K:K;K=K?K@K[K]K-X^K_K`K{K|K}K~KaLbLcLdLeLfLgLhLiLjLkLlLmLnLoLpLqLrLsLtLuLvLwLxLyLzLALBLCLDL.XELFLGLHLILJLKL/X:X;X=X?X@X[X]X^X_X`X{X|X}X~XaYbYcYdYeYfYgYhYLLMLNLiYOLPLQLRLSL8Jvw9Jww!Jxw#JZo'ljqjYkYlYmYnYoYpYqYrYsYtY(l)l}pkq$Jyw%J*l'J(J)J*J+J,J-J.J/J:JzwAwBwCwlqDwEwFwGwHwIwJw;JKw+lmq=JLw?JMwZg,l0gnquYvY@Jhh[JNw]JOwwYxYyYzYAYBYULVLWLXLCYYLDYurvrwrxryrzrArBrCrDrErKpFrGrHrIrJrKrLrMrNrOrPrQrRrSrTrUr1g2gEYFYGYHYIYJYKYLYMYNY]N^JOYPYEcZ FcQYPwRYZL0LSY1L2L3L4L5L6L7L8L9L!L#L$L4g2o5g6g3o7g8g9g1i!g#g$g9kybae2i(d%LTYUYVY%g'g(g)g*g+g,gGc-g.g/g:g;g=g?g@g[g]gHc^g_g`g{g|g}gIc~gahJcbh#r$r%r'r(r)r*r+r,r-r.r/r:r;r=r?r@rzV[r]r^r_r`r{r|r}r~rasbscsdsesfsgshs6A!k.b)d-lAVKq|iQwWiXiPpRwQpSwRpTwBVCVDVEVFVisjsGVHVkslsIVJVKVLVmsMVNVOVPVnsQVosRVpsSVTVqsUVVVrsWVXVsstsYVZV0V1Vus2V3V4V5V6V7Vvswsxs8Vys9V!Vzs_JAs#V$VBs%V'VCs(V)VDs*V+V,V-V.V/V:V;VEs=VFs?VGs@V[V]VHs^V_V`V{V|VIs}VJs~VaWKsLsbWMscWdWeW#k8kbeGbWYXY4kKc`JYY5k'LZtZYHh0YIh1YJh(L0t2Y} 3YYi4Yid)L6k*LKh+Lce,Ljd5Y/b6YLh7Y,f8YMh9Yde!YNh#Yee$YOh-Lfe%Ykd'Y:b(YPh.Lge)Y-f*Y/LLc+Y:L.f;L,Y/f=L-Y:f.Y?L;f@L[LMc/Y]L=f:Y;YQh=Yhe?Yld@Y;b[YRh^LSh]YTh_Lie^YUh_Yje`YVh`Lke{Lmd|L=b{YWh}Lle~L?f|Y@f}YXh~YndaMNcbMmeaZRyUwYh4o3gZi7kcMHbdMIbneeMfMgMbZ]c^c'b_cSphMiM/ljM:l;l=lkM?llMmMnMoMpMqMrMsMtMuM@l[l]lNsOsPsQsRsSs^l_l`l{l|l}l~lambmcmdmemfmgmhmimjmkmlmmmnmompmqmrmsmtmumvmwmxmymzmAmBmCmVwDmEmFmGmHmImJmKmLmMmNmOmPmQmRmSmTmUmAqVmWmXmYmZm0m1m2m3m4mTs5mcZ6mdZ3ieZ7mfZ8m~i?bTpvMwMajSybjcjdjTyLq9m!m#moepe1hUpUyUs$m%mej'mVs(mfj@bVpxMVygjWyhjijjjXy)m*m+m,mqere2hWpYyWs-m.mJbsetekj[f]f^fodue3h_f`fve9 wepdOcPcqd4hrdsdtdxeKb5hLbQc{f6hudvd~ abMb) * + , 7hbb|f}f~fag8h/m:mRcwdbgXp;m=m?mlj[bYpmjnjojpjZy@m[m]m^myeyMze9hZp0y_m`mqj!hNb{m1y#hXs$h%h'hYsrjsjtjujxd2yydcg|mZs0pvjwjxjcbzdAd(hAeBeCeScDedgEeFeyj)hOb}m3y*hzjAj+h0sBjCjDjEjBd4yCdeg~m1sFjGj,h-hGeHeIeJe.hKeLeMeNedbDdEdOePeQeFdfgReSean]b1pHjIjJjKjbncndnTeUe/h5yenfngghgigjggnhninjnkn:h^bkglgGdHdmgLjVeWeXeYeTcZeMj0e1e_bUcVcWcId`b{beb|b}b~blnacWwNjOjPjQj6ymnnnonpn2e3e;h2p7yqnrn0 PbQbbcXcYcZc0c- 1c2cJd4e5eKd6e7eRjcc=h?h8e9e@hsnngogpgtn!eLdqgunrgsgvndcSjTjUjVjwnxnyn#e$e[hznAn]htgfbWj2sug3pvgwgxg4p^h_h`h{h3c3s4c%eXj5p|h}hBnCnYjec6pzMAMZj8y0j1j2j9yDnEnFnGn'e(e~h7p!y4sHnInRb)e*e3jygzgAgMd+eaiBgCg,e! -eNd5c6cOdbiPdQdRd.eSb4jTb7ccidiSdTdgbhbUb. / : ; 5oibDgEgFgGgeiJnKn8cUdHg8pLnMnNn5jfc9p6j7j8j9j#yOnPnQnRn/eBM:efi5s$ySnTnUn!jgc!pCM#j%y$j%j'j'yVnWnXnYn;eDM=egi6s(y7sZn0n(jjbVdWdhi?e@e[e9c]eIg^e_e)jiiVb1n)yji*j+jki8s,j-j.j/jXd*yYdJg#p9s:j;jlimi`e{e|e}eni~eafbfcfkbZd0ddfefff1dKggfhf2nhc$p=j?j@j[j3n4n5nifjfoi+y6n7nLgMgNgOg8n9n!n#n$npiicPgQg2d3dRg]jkflfmfnf!cof^jpfqfjc#c$c%c4dkclclbmcncoc%npc%p_j`j{j|j,y'n(n)n*nrfsfqi!s-y+n,n1 WbXbqc'c(c)c*c= +c,c5dtfuf6dvfwf-nrc}j~jSgTgak'prisiti.nxfyfui(pviwi/nscbkckdkek:n;n=nzfAfxi?n@nyiUgmbfk#sVgXwWgXgYg)pziAiBiCi-c$s.cBf[n*pDiEi]nEMFM/c:c7d8d%s's^ngktc+pGM.yhk/yikjkkk:y_n`n{n|nCfDfFi,p-pHM(s)sIM;y.p}n~naolkuc/pJMKMmk=ynkokpk?ybocodoeoEfFfGi:p@y*sfogohoqkvc;pLM[yrk]ysktkuk^yiojokoloGfHfHi=p_y+smonooovkwc?pMM`ywk{yxkykzk|ypoqorosoIfJfIi@p}y,stouovoAkxc[pNM~yBkazCkDkEkbzwoxoyozoKfLfJi]pcz-sAoBoCoFkyc^pOMdzGkezHkIkJkfzDoEoFoGoMfNfKi_pgz.sHoIoJoKkzc`pPMQMLkhzMkNkOkizKoLoMoNoOfPfLi/s:sjz;sOoPoQoPkAc{pRMSMQkkzRkSkTklzRoSoToUoQfRfMi=s?smz@sVoWoTMUMVMWMXMgZYMZM0MhZ1M2MiZ3M4M5M6M7M8M9M!M#M$M%M'M(M)M*M+M,MjZ-M.M/M:M;M=M?M@M[M]M^M_M`MkZ{M|M}MlZ~MaNbNcNdNeNfNgNmZnZhNoZiNjNkNlNmNnN|pfWoNpNqNrNsNtNuNvNwNxNyNzNANBNCNDNENFNGNHNMqINJNKNLNMNatbtctdtetftgthtitjtktltmtntotptqtrtstttutvtwtxtytztAtBtCtDtEtFtGtHtItJtKtLtNNONPNMtNtOtQNRNSNTNUNVNWNXNpZYNZNqZrZ0N1N2NsZ3NtZ4N5N6NuZ7N8NSfNqTfOqUfVfWfPqQqXfYfRqSqTqZfUq0fVq1f2f3fWqXq4fYqZq0q1q5f2q6f7f8f9f!f#f3q4q$f9N!NvZwZxZyZ#NzZ$NAZ%N'N(N)N*NBZCZDZEZ+NFZ,NGZHZ-N.N/N:NIZ;N=N?N@N[NJZ

99  

100cdef CUresult cuCtxGetCurrent(CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

101 return cydriver._cuCtxGetCurrent(pctx) 2a kOlOmOnOoOpOqOrOsOtOuOvOwOxOyOzOAOBOCODOEOFOGOHOIOJOKOLOMONOOOPOQOROfBgBhBiBjBYwkBlBmBnBoBpBqBrBsBtBuBvBwBxByBzBSOABBBCBDBEB,tFBGBTOUOHBIBJBKBLB3 MB4 NB5 OB% PBZbQB0bRB1bSBBcTBVOUBVBWBXBYBZB0B1B2B3B4B5B6B7BWO-t.t8B9BXOdl!Bel#B$B,d%Bih'Bjh(Bkh)Blh*Bfl+Bgl,B-B.B/BYO/t:t:B;BZOll0Oml1O=B/d?Bmh@Bnh[Boh]Bph^Bnl2Ool3O_B`B{B|B}B~BaCbCcCdCeCfCgChCiCjCkC;t=tlCmCnCBloCClpCqC=drCqhsCrhtCshuCthvCDlwCElxCyCzCACBC?t@tCCDCECJlFCKlGCHC[dICuhJCvhKCwhLCxhMCJqNCLlOCPCQCRCSC[t]tTCUCVCQlWCRlXCYC_dZCyh0Czh1CAh2CBh3CSl4CTl5C6C7C8C9C^t_t!C#C$CYl%CZl'C(C|d)CCh*CDh+CEh,CFh-C0l.C1l/C:C;C=C?C@C[C]C^C_C`C{C|C4O}C~CaDbDcDdD[k5O6O7O8O9OZw!O#O$O%O'O(O)O*O+O]k,O-O.O/O:O;O=O?O@O6o[O7o]O8o^O9o_Osb`Otb{Oub|Ovb}O~OaPbPcPdPePfPgPhPiPjPkPlPmPnPoPpP!oqPrPsPtPuPvPwPxPyPzPb APBPDcCPDPEPFPGPHPIPJPKPLPMPNPOPPPQPRPSPTPtzuz1gUP2gVPWPXPYPZP0P1P2P3P4P5PQyVrvzwzxzyzzzAzBzCzgWDzWrEzFzGzHzIzJzKzLzMzNzOzPzXrQzRzSzTzUzVzWzXzYrYzZz0z1z2z3z4z5z6z7z8z9z!z#z$z%z'z(z)z*z+z,z-z.z/z:z;z=z?z@z[zZr0r]z^z_z`z{z|z}z~zaAbAcAdAeAfAgAhA1riAjAkAlAmAnAoApAqArAsA2rtAuAvAwAxAyAzAAA3rBACA4rDAEAFAGAHA5r6rIAJAKALA7rMANAOAPAQARASATAUA8rVAWAXA9rYAZA0A1A!r2A3A4A5A6P^J7P8P9PnzhWozKZpzEcZ Fc!P#P$P%P'P(P)P*P+P,P-P.P/P:P;P=P?Pae@P[P]P^PGcHcIcJc_P`P{P|P}P~PaQbQcQdQeQfQgQhQiQjQkQlQmQnQoQpQqQrQsQtQuQvQwQxQyQzQAQBQCQDQ.b-l|iisjskslsmsnsospsqsrssstsusvswsxsyszs_JAsBsCsDsEsFsGsHsIsJsKsLsMsbeEQFQGQHQIQJQKQLQMQNQOQPQQQRQSQTQUQVQWQXQYQZQ0Q1Q2Q3Q4Q5Q6Q7Q8Q9Q!Q#Q$Q%Q'Q(Q)Q*Q+Q,Q-Q.Q/Q:Q;Q=Q?Q@Q[Q]Q^Q_Q`Q{Q|Q}Q~QaRbRcRdReRfRgRhRYhiRjRIbkRlRmRnRSpoRpRqRrRsRtRuRvRwRghxRyRzRARBRCRDRERFRGRHRIRJRKRLRMRNRORPRQRRRSRTRURVRWRXRYRZR0R1R2R3R4R5R6R7R8R9R!R#R$R%R'R(R)R*R+R,R-R.R/R:R;R=R?R@R[R]R^R_R`R{R|R}R~RaSbScSdSeSfSgShSiSjSkSlSmSnSoSpSqSrSeDfDgDTphDsStSiDjD`t{tkDlDmD9mnD!moDuSpDpeqD1hrDvSsDtD$muD%mvDwDwSxDyDzDADVpBDxSySCDDD|t}tEDFDGD*mHD+mIDzSJDreKD2hLDASMDND-mOD.mPDQD~tauRDSD]fTD^fUDVDueWD3hXD_fYD`fZDbucuwedueuBqCqfuguhusdiutdju0Dku1DLbluQcmu2Dnuudouvdpuquru3D) 4D* 5D+ 6D, 7D7h8Dbb9D|f!D}fsu~ftuag#D8h$D/m%D:m'DRc(Dwd)Dbg*DXp+D;m,D=m-D.D/D:DYp;D=Duuvu?D@D[D[m]D]m^DBS_DCSze`D9h{DDS|D_m}D`m~DaEbEcE{mdEESeEfEwuxugEhEiEsjjEtjkEFSlEGSydmEcgnEHSoEpEvjqEwjrEsEtEyuzuuEvEBewECexEyEDezEdgAEEeBEFeCEAuBuCu}mDuDEEuFuGuHuIuJuCjKuDjLuEEMuFECdNuegOuGEPuFjQuGjRuSuTuGeUuHeVuIeWuJeXuYuKeZuLe0uMe1uNe2uHE3u4uIEPeJEQeKEFdLEfgMEReNESeOEPEQE1pRESE5u6uTEUEcnVEdnWEXEUeYE/hZE0Een1Efn2Egg3Ehg4Eig5Ejg6Egn7Ehn8Ein9Ejn!Ekn#E$E%Ekg'E(E7u8u)E*E+EWe,EXe-E.ETc/EZe:E;E0e=E1e?E@E9u!u[E]E`b^E{b_Eeb`E|b{E}b|E~b}E~EaFWwbFcF#u$udFeFfFnngFonhFISiF3ejF;hkFJSlFqnmFrnnF0 oFPb%uQb'ubcpFXcqFYcrFZcsF0ctF- uF1c(u2c)uJdvF4ewF5exFKdyF6ezF7eAFBFCF=hDFEF*u+uFFGFHFogIFpgJFKSKFLdLFqgMFNFrgOFsgPFQFRFSF,u-uTFUFxnVFynWFXF$eYF[hZFzn0FAn1F.u/u:uWj;u2F=u?uDqEq@u[u]u_h^u`h_u3F`u4F4c{u%e|u5F}u|h~u}havBn6F7F8F9F6p!FLSMS#F$Fbvcv%F'F(FEn)FFn*FNS+F(e,F~h-FOS.F/FHn:FIn;F=Fdvev?F@Fzg[FAg]F^F+e_Fai`FBg{FCg|Ffvgv-ehvivFqGqjvkvlvQdmvRdnv}Fov~FTbpv7cqvaGrvSdsvTdtvuvvvbG. cG/ dG: eG; fG5ogGibhGDgiGEgwvFgxvGgjGeikGJnlGKnmG8cnGUdoGHgpG8pqGLnrGMnsGtGuGvG9pwGxGyvzvyGzGAGPnBGQnCGPSDGQS:eEGfiFGRSGGSnHGTnIGJGKGLG!pMGSSNGOGAvBvPGQGRGWnSGXnTGTSUGUS=eVGgiWGVSXGYGZnZG0n0G1G2GCvDv3G4G@e5G[e6G7G]e8GIg9G^e!G_e#GEvFvGv1nHv$GIvJvKvLvMvNv-jOv.jPv%GQv'GYdRvJgSv(GTv:jUv;jVvWvXv`eYv{eZv|e0v}e1v2v~e3vaf4vbf5vcf6v)G7v8v*Gef+Gff,G1d-GKg.Ggf/Ghf:G;G=G$p?G@G9v!v[G]G4n^G5n_G`Gjf{Goi|G}G6n~G7naHLgbHMgcHNgdHOgeH8nfH9ngH!nhH#niH$njHkHlHPgmHnH#v$voHpHqHlfrHmfsHtH!cuHofvHwHpfxHqfyHzH%v'vAHBHkcCHlcDHlbEHmcFHncGHocHHIHJH%pKHLH(v)vMHNHOH(nPH)nQHWSRHsfSHqiTHXSUH+nVH,nWH1 XHWb*vXb+vqcYH'cZH(c0H)c1H*c2H= 3H+c,v,c-v5d4Htf5Huf6H6d7Hvf8Hwf9H!H#H}j$H%H.v/v'H(H)Hsi*Hti+HYS,Hyf-Hui.H/Hvi:Hwi;H=H?H@H:v;v[H]H;n^H=n_H`HAf{Hxi|H?n}H@n~H=v?v@vfk[vaI]v^vHqIq_v`v{vAi|vBi}vbI~vcI.cawBfbwdIcwDidwEiew]neIZS0S1S2SfIgIhI+piI3S4SjIkIfwgwlImInI`noI{npI5SqIDfrIFisI6S7S8S9S!S#StIuI}nvI~nwIxIyIzI/pAI$S%SBICIhwiwDIEIFIcoGIdoHI'SIIFfJIGiKI(SLIMIfoNIgoOIPIQIRI;pSI)S*STIUIjwkwVIWIXIjoYIkoZI+S0IHf1IHi2I,S3I4Imo5Ino6I7I8I9I?p!I-S.S#I$Ilwmw%I'I(Iqo)Iro*I/S+IJf,IIi-I:S.I/Ito:Iuo;I=I?I@I[p[I;S=S]I^Inwow_I`I{Ixo|Iyo}I?S~ILfaJJibJ@ScJdJAoeJBofJgJhJiJ^pjJ[S]SkJlJpwqwmJnJoJEopJFoqJ^SrJNfsJKitJ_SuJvJHowJIoxJyJzJAJ`pBJ`S{SCJDJrwswEJFJGJLoHJMoIJ|SJJPfKJLiLJ}S~SMJNJOoOJPoPJQJRJSJ{pTJaTbTUJVJtwuwWJXJYJSoZJTo0JcT1JRf2JMi3JdTeT4J5JVo6JWo7JfTgT[shTiTjTkTlTmTnToTpTqTrTsTtTuTvTwTxTyTzTATBTCTDTETFTGTHTITJTKTLTMTNTOTPTQTRTSTTTUTVT]s^sJpWTXTYTZT0T1T2T3T4T5T6T7T8T9T_s`siW{sjWkW!TlW|s}s~smW#T$T%T'T(T)T*T+T,T|p-T.T/T:T;T=T?T@T[T0i]T^T_T`T{T|T}T~TaUbUcUdUeUfUgUhUiUjUkUlUmUnUoUpUqUrUsUtUuUvUwUxUyUzUAUBUCUDUEUFUGUHUIUJUKULUMUNUOUPUQURUSUTUUUVUWUXUYUZU0U1U2U3U4U5U6U7U8U9U!U#U$U%U'U(U)U*U+U,U-U.U/U:U;U=USfTfUfVfWfXfYfZf0f1f2f3f4f5f6f7f8f9f!f#f$f?U@U[U]U^U_U`U{U|U}U~UaVbVcVdVeVfVgVhViVjVkVlVmVnVoVpVqVrVsVtVuVvVwVxV

102  

103cdef CUresult cuCtxGetDevice(CUdevice* device) except ?CUDA_ERROR_NOT_FOUND nogil: 

104 return cydriver._cuCtxGetDevice(device) 2a ^NzbAb*fR S 4i2 W $ nbc d e f g h i j k l m n o p q v r s t u G H I J qzrz~pLZrrXtszYt`k!i{k#i|k}kaq`c;c=c?c9dX !b{c|cobpbqbYbrb3 4 5 % Zb0b1bBcbqcqdqeqfqgqQi2k~kal(b$i*d+d%ibd,dihjhkhlhhlil)b'i-d.d(icd/dmhnhohphpl)iql*irlsltl+iul,ivlwlxlyl*b-i:d;d.idd=dqhrhshthFlGl+b/i?d@d:ied[duhvhwhxhMlNl,b;i]d^d=ifd_dyhzhAhBhUlVl-b?i`d{d@igd|dChDhEhFh2l[i3l]i4l5l6l^i7l_i8l9l!l`i#l{i$l%l3khq!d@c_N`N{N|N}N~Nsbtbubvb#b$b2bch#d5iBbCb$d6iiq(fT ? @ 3b%bM L z A B b w ( x y D ' E F O P Q C U V wb4b5b[c6bN vwwwxwZojqkqywzwAwBwCwlqDwEwFwGwHwIwJwKwmqLwMwnqhhNwOw5q6q7q8q9q!qtzuz1g2g{J0wQyVrvzwzxzyzzzAzBzCzgWDzWrEzFzGzHzIzJzKzLzMzNzOzPzXrQzRzSzTzUzVzWzXzYrYzZz0z1z2z3z4z5z6z7z8z9z!z#z$z%z'z(z)z*z+z,z-z.z/z:z;z=z?z@z[zZr0r]z^z_z`z{z|z}z~zaAbAcAdAeAfAgAhA1riAjAkAlAmAnAoApAqArAsA2rtAuAvAwAxAyAzAAA3rBACA4rDAEAFAGAHA5r6rIAJAKALA7rMANAOAPAQARASATAUA8rVAWAXA9rYAZA0A1A!r2A3A4A5A^JnzhWozpzEcZ Fc|JPw}J$k%k'k(k)k*kxb+k,k-k.k7i/kdhCcMZybae2i(daONZ8i%g'g(g)g*g+g,gGc-g.g/g:g;g=g?g@g[g]gHc^g_g`g{g|g}gIc~gahJcbhOZ#r$r%rPZ'r(r)r*r+r,r-r.r/r:r;r=r?r@rzV[r]r^r_r`r{r|r}r~rasbscsdsesfsgshs6A!k.b)d-lAVKq|iQwBVCVDVEVFVisjsGVHVkslsIVJVKVLVmsMVNVOVPVnsQVosRVpsSVTVqsUVVVrsWVXVsstsYVZV0V1Vus2V3V4V5V6V7Vvswsxs8Vys9V!Vzs_JAs#V$VBs%V'VCs(V)VDs*V+V,V-V.V/V:V;VEs=VFs?VGs@V[V]VHs^V_V`V{V|VIs}VJs~VaWKsLsbWMscWdWeW#k8kbeGbQZ4kKc`J5kZtHhIhJh0t} Yiid6kRZKhcejd/bLh,fMhdeNheeOhfekd:bPhge-f7ALc8A.f9A/f!A:f#A;f$AMc%A=f'AQhheld;bRhShThieUhjeVhkemd=bWhle?f@fXhndNcmeUwYh4o3gZi7kHbIbne.lZh0hbO]c^c'b_cSpcOoq/lpq:lnW;loW=lK ?lghqqrqsqtquqvqwqxqyqzq@l[l]lNsOsPsQsRsSs(A^l)A_l*A`l+A{l,A|l-A}l1t~l2tam3tbm4tcm5tdm6tem7tfm8tgm9thm!tim#tjm$tkm%tlm'tmm(tnm)tom*tpm+tqmSZrmTZsm.Atm/Aum:Avm;Awm=Axm?Aym@Azm[AAm]ABm^ACm_AVw`ADm{AEm|AFm}AGm~AHmaBImbBJmcBKmdBLmeBMmUZNmpWOmqWPmrWQmsWRmtWSmuWTmvWUmwWAqxWVmyWWmzWXmAWYmBWZmCW0mDW1mEW2m3m8m?bajdj#moepe1hUp'm(m@bgjjj,mqere2hWpJbsetekj[f]f^fodue3h_f`fve9 pdqdxeKbLbQc{f~ abMb) * + , 7hbb|fagRcwdbg?m[bmjpj^myeze9hZpqjNb#h'hujxdydcg|mxjcbzdAd(hAeBeCeScDedgEeFeyjOb*h+hEjBdCdeg~mdbDdEdOePeQeFdfgReSean]bHjKjTeUe/h:h^bkglgGdHdmgLjVeWeXeYeTcZeMj0e1e_bUcVcWcId`b{beb|b}b~blnacNjQjpn2e3e;h2p0 PbQbbcXcYcZc0c- 1c2cJd4e5eKd6e7eRjcc=h?h8e9e@hsnngogpgtn!eLdqgunrgsgvndcSjVj#e$e[h]hfbugxg{h3c4c%eXjCnecZj2jGn'e(e~h7pRb)e*e3jygzgAgMd+eaiBgCg,e! NdOd.eSbTb7ccigbhbUb. / : ; 5oibDgGg8cUdHgNnfc6j9jRn/e:efi5sUngc#j'jYn;e=egi6s(jjbVdWdhi?e@e[e9c]eIg^e_e)jVbjiki/jXdYdJg#pkbZd0ddfefff1dKggfhf2nhc=j[jifjfoipiicPgQg2d3dRg]jkflfmfnf!cof^jpfqfjc#c$c%c4dkclclbmcncoc%npc_j|j*nrfsfqi!s1 WbXbqc'c(c)c*c= +c,c5dtfuf6dvfwf-nrc}j~jSgTgak'prisiti.nxfyfui(pviwi/nscbkekzfAfxiyimbVgYgCi-c.cBf[n%s's^ntchkkk|nCfDfFi,p-p(s)saoucmkpkeoEfFfGi:phovcrkukloGfHfHi=poowcwkzksoIfJfIi@pvoxcBkEkzoKfLfJi]pCoycGkJkGoMfNfKi_pJozcLkOkNoOfPfLi/s:sQoAcQkTkUoQfRfMi=s?sdOeO[sfOgOhOiO]s^sJp_s`siW{sjWkWVZlW|s}s~smWWZ|pfWXZ#q1w2w3w4w5w0i6w7w8w9w!w#w$w%w'w:k(wMq$q)weh*watbtctdtetftgthtitjtktltmtntotptqtrtstttutvtwtxtytztAtBtCtDtEtFtGtHtItJtKtLtMtNtOtYZZZ0Z1Z2Z3Z4Z5Z6Z7Z8Z9Z!Z#Z$Z%Z'Z(Z)Z*Z+Z,Z-Z.ZSfNqTfOqUfVfWfPqQqXfYfRqSqTqZfUq0fVq1f2f3fWqXq4fYqZq0q1q5f2q6f7f8f9f!f#f3q4q$f/Z:Z

105  

106cdef CUresult cuCtxGetDevice_v2(CUdevice* device, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

107 return cydriver._cuCtxGetDevice_v2(device, ctx) 

108  

109cdef CUresult cuCtxGetFlags(unsigned int* flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

110 return cydriver._cuCtxGetFlags(flags) 

111  

112cdef CUresult cuCtxSetFlags(unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

113 return cydriver._cuCtxSetFlags(flags) 

114  

115cdef CUresult cuCtxGetId(CUcontext ctx, unsigned long long* ctxId) except ?CUDA_ERROR_NOT_FOUND nogil: 

116 return cydriver._cuCtxGetId(ctx, ctxId) 

117  

118cdef CUresult cuCtxSynchronize() except ?CUDA_ERROR_NOT_FOUND nogil: 

119 return cydriver._cuCtxSynchronize() 

120  

121cdef CUresult cuCtxSynchronize_v2(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

122 return cydriver._cuCtxSynchronize_v2(ctx) 

123  

124cdef CUresult cuCtxSetLimit(CUlimit limit, size_t value) except ?CUDA_ERROR_NOT_FOUND nogil: 

125 return cydriver._cuCtxSetLimit(limit, value) 

126  

127cdef CUresult cuCtxGetLimit(size_t* pvalue, CUlimit limit) except ?CUDA_ERROR_NOT_FOUND nogil: 

128 return cydriver._cuCtxGetLimit(pvalue, limit) 

129  

130cdef CUresult cuCtxGetCacheConfig(CUfunc_cache* pconfig) except ?CUDA_ERROR_NOT_FOUND nogil: 

131 return cydriver._cuCtxGetCacheConfig(pconfig) 

132  

133cdef CUresult cuCtxSetCacheConfig(CUfunc_cache config) except ?CUDA_ERROR_NOT_FOUND nogil: 

134 return cydriver._cuCtxSetCacheConfig(config) 

135  

136cdef CUresult cuCtxGetApiVersion(CUcontext ctx, unsigned int* version) except ?CUDA_ERROR_NOT_FOUND nogil: 

137 return cydriver._cuCtxGetApiVersion(ctx, version) 

138  

139cdef CUresult cuCtxGetStreamPriorityRange(int* leastPriority, int* greatestPriority) except ?CUDA_ERROR_NOT_FOUND nogil: 

140 return cydriver._cuCtxGetStreamPriorityRange(leastPriority, greatestPriority) 2zbAb*fR S 4i2 W $ nbc d e f g h i j k l m n o p q v r s t u G H I J `c;c=c?c9dX !b{c|cobpbqbYbrb3 4 5 % Zb0b1bBc@c#b$bBbCbT ? @ %bM L z A B b 7b8b9b}c~cadw ( x y D ' E F O P Q DbEbFb6 7 8 C U V wb4b5b[c6bN Y # UkVkWkXkYkZk0k1k;k~JaK+fNiZg0g%f'fOiPi] ^ _ ` { | 5q6q7q8q9q!q0wEcZ Fc$k%k'k(k)k*kxb+k,k-k.k7i/kdhCc4g2o5g6g3o7g8g9g1i!g#g$g9kybae2i(d8i.b)d%q'q#o(q$o)q*q%o'o+q,q-q(o.q)o*o+o,o-o.o/o:o;o/q=o?o@o[o:q]o^o;q=q?q@q_o[q`o]q^q{o|o_q`q{q}o|q~oapbpcpdpepfpgphp}qipjpkplp~qmpnparbrcrdroperppfrgrqprphrirjrspkrtpupvpwpxpypzpApBplrCpDpEpFpmrGpHpnrorGb} 4oHbK 3iUsVsWs0p]htgfbWj2sug3pvgwgxg4p^h_h`h{h3c3s4c%eXj5p|h}h4s7syiUgmbfk#sVgXwWgXgYg)pziAiBiCi-c$s.cBf[n*pDiEi7d8d.p*s+s,s-s.s;s@s#q1w2w3w4w5w0i6w7w8w9w!w#w$w%w'w:k(wMq$q)weh*w

141  

142cdef CUresult cuCtxResetPersistingL2Cache() except ?CUDA_ERROR_NOT_FOUND nogil: 

143 return cydriver._cuCtxResetPersistingL2Cache() 

144  

145cdef CUresult cuCtxGetExecAffinity(CUexecAffinityParam* pExecAffinity, CUexecAffinityType typename) except ?CUDA_ERROR_NOT_FOUND nogil: 

146 return cydriver._cuCtxGetExecAffinity(pExecAffinity, typename) 

147  

148cdef CUresult cuCtxRecordEvent(CUcontext hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil: 

149 return cydriver._cuCtxRecordEvent(hCtx, hEvent) 

150  

151cdef CUresult cuCtxWaitEvent(CUcontext hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil: 

152 return cydriver._cuCtxWaitEvent(hCtx, hEvent) 

153  

154cdef CUresult cuCtxAttach(CUcontext* pctx, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

155 return cydriver._cuCtxAttach(pctx, flags) 

156  

157cdef CUresult cuCtxDetach(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

158 return cydriver._cuCtxDetach(ctx) 

159  

160cdef CUresult cuCtxGetSharedMemConfig(CUsharedconfig* pConfig) except ?CUDA_ERROR_NOT_FOUND nogil: 

161 return cydriver._cuCtxGetSharedMemConfig(pConfig) 

162  

163cdef CUresult cuCtxSetSharedMemConfig(CUsharedconfig config) except ?CUDA_ERROR_NOT_FOUND nogil: 

164 return cydriver._cuCtxSetSharedMemConfig(config) 

165  

166cdef CUresult cuModuleLoad(CUmodule* module, const char* fname) except ?CUDA_ERROR_NOT_FOUND nogil: 

167 return cydriver._cuModuleLoad(module, fname) 

168  

169cdef CUresult cuModuleLoadData(CUmodule* module, const void* image) except ?CUDA_ERROR_NOT_FOUND nogil: 

170 return cydriver._cuModuleLoadData(module, image) 2%d'dRiSiTi)fUiVi

171  

172cdef CUresult cuModuleLoadDataEx(CUmodule* module, const void* image, unsigned int numOptions, CUjit_option* options, void** optionValues) except ?CUDA_ERROR_NOT_FOUND nogil: 

173 return cydriver._cuModuleLoadDataEx(module, image, numOptions, options, optionValues) 2;Z

174  

175cdef CUresult cuModuleLoadFatBinary(CUmodule* module, const void* fatCubin) except ?CUDA_ERROR_NOT_FOUND nogil: 

176 return cydriver._cuModuleLoadFatBinary(module, fatCubin) 

177  

178cdef CUresult cuModuleUnload(CUmodule hmod) except ?CUDA_ERROR_NOT_FOUND nogil: 

179 return cydriver._cuModuleUnload(hmod) 2%d'dRiSiTi)fUiVi

180  

181cdef CUresult cuModuleGetLoadingMode(CUmoduleLoadingMode* mode) except ?CUDA_ERROR_NOT_FOUND nogil: 

182 return cydriver._cuModuleGetLoadingMode(mode) 

183  

184cdef CUresult cuModuleGetFunction(CUfunction* hfunc, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil: 

185 return cydriver._cuModuleGetFunction(hfunc, hmod, name) 2%d'dRiSiTi)fUiVi

186  

187cdef CUresult cuModuleGetFunctionCount(unsigned int* count, CUmodule mod) except ?CUDA_ERROR_NOT_FOUND nogil: 

188 return cydriver._cuModuleGetFunctionCount(count, mod) 

189  

190cdef CUresult cuModuleEnumerateFunctions(CUfunction* functions, unsigned int numFunctions, CUmodule mod) except ?CUDA_ERROR_NOT_FOUND nogil: 

191 return cydriver._cuModuleEnumerateFunctions(functions, numFunctions, mod) 

192  

193cdef CUresult cuModuleGetGlobal(CUdeviceptr* dptr, size_t* numbytes, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil: 

194 return cydriver._cuModuleGetGlobal_v2(dptr, numbytes, hmod, name) 2)f

195  

196cdef CUresult cuLinkCreate(unsigned int numOptions, CUjit_option* options, void** optionValues, CUlinkState* stateOut) except ?CUDA_ERROR_NOT_FOUND nogil: 

197 return cydriver._cuLinkCreate_v2(numOptions, options, optionValues, stateOut) 

198  

199cdef CUresult cuLinkAddData(CUlinkState state, CUjitInputType typename, void* data, size_t size, const char* name, unsigned int numOptions, CUjit_option* options, void** optionValues) except ?CUDA_ERROR_NOT_FOUND nogil: 

200 return cydriver._cuLinkAddData_v2(state, typename, data, size, name, numOptions, options, optionValues) 

201  

202cdef CUresult cuLinkAddFile(CUlinkState state, CUjitInputType typename, const char* path, unsigned int numOptions, CUjit_option* options, void** optionValues) except ?CUDA_ERROR_NOT_FOUND nogil: 

203 return cydriver._cuLinkAddFile_v2(state, typename, path, numOptions, options, optionValues) 

204  

205cdef CUresult cuLinkComplete(CUlinkState state, void** cubinOut, size_t* sizeOut) except ?CUDA_ERROR_NOT_FOUND nogil: 

206 return cydriver._cuLinkComplete(state, cubinOut, sizeOut) 

207  

208cdef CUresult cuLinkDestroy(CUlinkState state) except ?CUDA_ERROR_NOT_FOUND nogil: 

209 return cydriver._cuLinkDestroy(state) 

210  

211cdef CUresult cuModuleGetTexRef(CUtexref* pTexRef, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil: 

212 return cydriver._cuModuleGetTexRef(pTexRef, hmod, name) 

213  

214cdef CUresult cuModuleGetSurfRef(CUsurfref* pSurfRef, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil: 

215 return cydriver._cuModuleGetSurfRef(pSurfRef, hmod, name) 

216  

217cdef CUresult cuLibraryLoadData(CUlibrary* library, const void* code, CUjit_option* jitOptions, void** jitOptionsValues, unsigned int numJitOptions, CUlibraryOption* libraryOptions, void** libraryOptionValues, unsigned int numLibraryOptions) except ?CUDA_ERROR_NOT_FOUND nogil: 

218 return cydriver._cuLibraryLoadData(library, code, jitOptions, jitOptionsValues, numJitOptions, libraryOptions, libraryOptionValues, numLibraryOptions) 2R S 2 W $ nbc d e f g h i j k l m n o p q v r s t u G H I J X obpbqbYbrbQi2k(bbd)bcd*bdd+bed,bfd-bgd!dsbtbubvb2biq(fT ? @ 3bM L z A B b w ( x y D ' E F O P Q C U V wb4b5b[c6bN Y # Z xbCcyb(d8i%g'g(g)g*g+g,gGc-g.g/g:g;g=g?g@g[g]gHc^g_g`g{g|g}gIc~gahJcbhoq/lpq:l;l=lK ?lghqqrqsqtquqvqwqxqyqzq@l[lFW]lGW=Z^l_l`l{l|l}l~lambmcmdmemfmgmhmimjmkmlmmmnmompmqmrmsmtmumvmwmxmymzmAmBmCmVwDmEmFmGmHmImJmKmLmMmNmOmPmQmRmSmTmUmAqVmWmXmYmZm0m1m2m3m?b#moeUp'm@b,mqeWpJbod9 xeKb{f~ abMb) * + , bbRc[b^myeZpNbujxd|mcbScObEjBd~mdb]bTe:h^bkglgGdHdmgLjVeWeXeYeTcZeMj0e1e_bUcVcWcId`b{beb|b}b~bacpn2e2p0 - Rjcc=h?h8e9e@hsnngogpgtn!eLdqgunrgsgdc#efb{h3cXjecGn'e7pRbMd! .eSbgbhbUb. / : ; ib8cfcRn/egcYn;ejb9cVb/jXdkbhcifpiicPgQg2d3dRg]jkflfmfnf!cof^jpfqfjc#c$c%c4dkclclbmcncocpc*nrf1 = rc.nxfsczfmbCi-ctc|nCf,p-puceoEf:pvcloGf=pwcsoIf@pxczoKf]pycGoMf_pzcNoOfAcUoQfJp

219  

220cdef CUresult cuLibraryLoadFromFile(CUlibrary* library, const char* fileName, CUjit_option* jitOptions, void** jitOptionsValues, unsigned int numJitOptions, CUlibraryOption* libraryOptions, void** libraryOptionValues, unsigned int numLibraryOptions) except ?CUDA_ERROR_NOT_FOUND nogil: 

221 return cydriver._cuLibraryLoadFromFile(library, fileName, jitOptions, jitOptionsValues, numJitOptions, libraryOptions, libraryOptionValues, numLibraryOptions) 2HWIW

222  

223cdef CUresult cuLibraryUnload(CUlibrary library) except ?CUDA_ERROR_NOT_FOUND nogil: 

224 return cydriver._cuLibraryUnload(library) 

225  

226cdef CUresult cuLibraryGetKernel(CUkernel* pKernel, CUlibrary library, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil: 

227 return cydriver._cuLibraryGetKernel(pKernel, library, name) 2R S 2 W $ nbc d e f g h i j k l m n o p q v r s t u G H I J X obpbqbYbrbQi2k(bbd)bcd*bdd+bed,bfd-bgd!dsbtbubvb2biq(fT ? @ 3bM L z A B b w ( x y D ' E F O P Q C U V wb4b5b[c6bN Y # Z xbCcyb(d8i%g'g(g)g*g+g,gGc-g.g/g:g;g=g?g@g[g]gHc^g_g`g{g|g}gIc~gahJcbhoq/lpq:l;l=lK ?lghqqrqsqtquqvqwqxqyqzq@lHW[lFW]lIWGW^l_l`l{l|l}l~lambmcmdmemfmgmhmimjmkmlmmmnmompmqmrmsmtmumvmwmxmymzmAmBmCmVwDmEmFmGmHmImJmKmLmMmNmOmPmQmRmSmTmUmAqVmWmXmYmZm0m1m2m3m?b#moe'm@b,mqeJbod9 xeKb~ abMb) * + , bbRc[b^myeNbujxdcbScObEjBddb]bTe:h^bkglgGdHdmgLjVeWeXeYeTcZeMj0e1e_bUcVcWcId`b{beb|b}b~bacpn2e0 - cctn!edc#efb{h3cecGn'eRbMd! .eSbgbhbUb. / : ; ib8cfcRn/egcYn;ejb9cVb/jXdkbhcifpiicPgQg2d3dRg]jkflfmfnf!cof^jpfqfjc#c$c%c4dkclclbmcncocpc*nrf1 = rc.nxfsczfmbCi-ctc|nCfuceoEfvcloGfwcsoIfxczoKfycGoMfzcNoOfAcUoQfJp

228  

229cdef CUresult cuLibraryGetKernelCount(unsigned int* count, CUlibrary lib) except ?CUDA_ERROR_NOT_FOUND nogil: 

230 return cydriver._cuLibraryGetKernelCount(count, lib) 

231  

232cdef CUresult cuLibraryEnumerateKernels(CUkernel* kernels, unsigned int numKernels, CUlibrary lib) except ?CUDA_ERROR_NOT_FOUND nogil: 

233 return cydriver._cuLibraryEnumerateKernels(kernels, numKernels, lib) 

234  

235cdef CUresult cuLibraryGetModule(CUmodule* pMod, CUlibrary library) except ?CUDA_ERROR_NOT_FOUND nogil: 

236 return cydriver._cuLibraryGetModule(pMod, library) 

237  

238cdef CUresult cuKernelGetFunction(CUfunction* pFunc, CUkernel kernel) except ?CUDA_ERROR_NOT_FOUND nogil: 

239 return cydriver._cuKernelGetFunction(pFunc, kernel) 

240  

241cdef CUresult cuKernelGetLibrary(CUlibrary* pLib, CUkernel kernel) except ?CUDA_ERROR_NOT_FOUND nogil: 

242 return cydriver._cuKernelGetLibrary(pLib, kernel) 

243  

244cdef CUresult cuLibraryGetGlobal(CUdeviceptr* dptr, size_t* numbytes, CUlibrary library, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil: 

245 return cydriver._cuLibraryGetGlobal(dptr, numbytes, library, name) 

246  

247cdef CUresult cuLibraryGetManaged(CUdeviceptr* dptr, size_t* numbytes, CUlibrary library, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil: 

248 return cydriver._cuLibraryGetManaged(dptr, numbytes, library, name) 

249  

250cdef CUresult cuLibraryGetUnifiedFunction(void** fptr, CUlibrary library, const char* symbol) except ?CUDA_ERROR_NOT_FOUND nogil: 

251 return cydriver._cuLibraryGetUnifiedFunction(fptr, library, symbol) 

252  

253cdef CUresult cuKernelGetAttribute(int* pi, CUfunction_attribute attrib, CUkernel kernel, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

254 return cydriver._cuKernelGetAttribute(pi, attrib, kernel, dev) 2iq(fT oqpqnWoW1t2t3t4t5t6t7t8t9t!t#t$t%t't(t)t*t+tpWqWrWsWtWuWvWwWxWyWzWAWBWCWDWEW

255  

256cdef CUresult cuKernelSetAttribute(CUfunction_attribute attrib, int val, CUkernel kernel, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

257 return cydriver._cuKernelSetAttribute(attrib, val, kernel, dev) 

258  

259cdef CUresult cuKernelSetCacheConfig(CUkernel kernel, CUfunc_cache config, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

260 return cydriver._cuKernelSetCacheConfig(kernel, config, dev) 

261  

262cdef CUresult cuKernelGetName(const char** name, CUkernel hfunc) except ?CUDA_ERROR_NOT_FOUND nogil: 

263 return cydriver._cuKernelGetName(name, hfunc) 2?Z

264  

265cdef CUresult cuKernelGetParamInfo(CUkernel kernel, size_t paramIndex, size_t* paramOffset, size_t* paramSize) except ?CUDA_ERROR_NOT_FOUND nogil: 

266 return cydriver._cuKernelGetParamInfo(kernel, paramIndex, paramOffset, paramSize) 2K ghqqrqsqtquqvqwqxqyqzq@Z

267  

268cdef CUresult cuKernelGetParamCount(CUkernel kernel, size_t* paramCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

269 return cydriver._cuKernelGetParamCount(kernel, paramCount) 

270  

271cdef CUresult cuMemGetInfo(size_t* free, size_t* total) except ?CUDA_ERROR_NOT_FOUND nogil: 

272 return cydriver._cuMemGetInfo_v2(free, total) 

273  

274cdef CUresult cuMemAlloc(CUdeviceptr* dptr, size_t bytesize) except ?CUDA_ERROR_NOT_FOUND nogil: 

275 return cydriver._cuMemAlloc_v2(dptr, bytesize) 2+wJW[ KWLWMWNWOWPWQWRWSWTWUW%d'd!k.b)d-lQw%q'q#o(q$o)q*q%o'o+q,q-q(o.q)o*o+o,o-o.o/o:o;o/q=o?o@o[o:q]o^o;q=q#kUwYh4o

276  

277cdef CUresult cuMemAllocPitch(CUdeviceptr* dptr, size_t* pPitch, size_t WidthInBytes, size_t Height, unsigned int ElementSizeBytes) except ?CUDA_ERROR_NOT_FOUND nogil: 

278 return cydriver._cuMemAllocPitch_v2(dptr, pPitch, WidthInBytes, Height, ElementSizeBytes) 

279  

280cdef CUresult cuMemFree(CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil: 

281 return cydriver._cuMemFree_v2(dptr) 2w ( x y D ' E F O P Q hd] ^ _ ` { | 0o+wprJW[ KWLWMWNWOWPWQWRWSWTWGhybae2iUW%d'd!k.b)d-l|iQwPpRw%q'q#o(q$o)q*q%o'o+q,q-q(o.q)o*o+o,o-o.o/o:o;o/q=o?o@o[o:q]o^o;q=qcrdroperppfrgrqprphrirjrspkrtpupvpwpxpypzpApBplrCpDpEpFpmrGpHpnror#k4kUwYh4oK

282  

283cdef CUresult cuMemGetAddressRange(CUdeviceptr* pbase, size_t* psize, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil: 

284 return cydriver._cuMemGetAddressRange_v2(pbase, psize, dptr) 

285  

286cdef CUresult cuMemAllocHost(void** pp, size_t bytesize) except ?CUDA_ERROR_NOT_FOUND nogil: 

287 return cydriver._cuMemAllocHost_v2(pp, bytesize) 2R W c d e f g h i j k l m n o p q v r s t u G H I J M L z A B b DcC U V Y # Z xbyb%g'g(g)g*g+g,gGc-g.g/g:g;g=g?g@g[g]gHc^g_g`g{g|g}gIc~gahJcbh!k.b)dKqQpSw?q@q_o[q`o]q^q{o|o_q`q{q}o|q~oapbpcpdpepfpgphp}qipjpkplp~qmpnparbr#kK

288  

289cdef CUresult cuMemFreeHost(void* p) except ?CUDA_ERROR_NOT_FOUND nogil: 

290 return cydriver._cuMemFreeHost(p) 2R W c d e f g h i j k l m n o p q v r s t u G H I J M L z A B b DcC U V hdVWWWZ xbyb%g'g(g)g*g+g,gGc-g.g/g:g;g=g?g@g[g]gHc^g_g`g{g|g}gIc~gahJcbh!k.b)dKqQpSw?q@q_o[q`o]q^q{o|o_q`q{q}o|q~oapbpcpdpepfpgphp}qipjpkplp~qmpnparbr#kK

291  

292cdef CUresult cuMemHostAlloc(void** pp, size_t bytesize, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

293 return cydriver._cuMemHostAlloc(pp, bytesize, Flags) 2VWWW

294  

295cdef CUresult cuMemHostGetDevicePointer(CUdeviceptr* pdptr, void* p, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

296 return cydriver._cuMemHostGetDevicePointer_v2(pdptr, p, Flags) 

297  

298cdef CUresult cuMemHostGetFlags(unsigned int* pFlags, void* p) except ?CUDA_ERROR_NOT_FOUND nogil: 

299 return cydriver._cuMemHostGetFlags(pFlags, p) 

300  

301cdef CUresult cuMemAllocManaged(CUdeviceptr* dptr, size_t bytesize, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

302 return cydriver._cuMemAllocManaged(dptr, bytesize, flags) 2w ( x y D ' E F O P Q Y # +fNiZg0g%f'fOiPi] ^ _ ` { | 0oprybae2i!k.b)d|iPpRwcrdroperppfrgrqprphrirjrspkrtpupvpwpxpypzpApBplrCpDpEpFpmrGpHpnror#k4k

303  

304cdef CUresult cuDeviceRegisterAsyncNotification(CUdevice device, CUasyncCallback callbackFunc, void* userData, CUasyncCallbackHandle* callback) except ?CUDA_ERROR_NOT_FOUND nogil: 

305 return cydriver._cuDeviceRegisterAsyncNotification(device, callbackFunc, userData, callback) 

306  

307cdef CUresult cuDeviceUnregisterAsyncNotification(CUdevice device, CUasyncCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil: 

308 return cydriver._cuDeviceUnregisterAsyncNotification(device, callback) 

309  

310cdef CUresult cuDeviceGetByPCIBusId(CUdevice* dev, const char* pciBusId) except ?CUDA_ERROR_NOT_FOUND nogil: 

311 return cydriver._cuDeviceGetByPCIBusId(dev, pciBusId) 

312  

313cdef CUresult cuDeviceGetPCIBusId(char* pciBusId, int length, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

314 return cydriver._cuDeviceGetPCIBusId(pciBusId, length, dev) 

315  

316cdef CUresult cuIpcGetEventHandle(CUipcEventHandle* pHandle, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil: 

317 return cydriver._cuIpcGetEventHandle(pHandle, event) 2Y # UkVkWkXkYkZk0k1k;k3i7d8d

318  

319cdef CUresult cuIpcOpenEventHandle(CUevent* phEvent, CUipcEventHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil: 

320 return cydriver._cuIpcOpenEventHandle(phEvent, handle) 

321  

322cdef CUresult cuIpcGetMemHandle(CUipcMemHandle* pHandle, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil: 

323 return cydriver._cuIpcGetMemHandle(pHandle, dptr) 

324  

325cdef CUresult cuIpcOpenMemHandle(CUdeviceptr* pdptr, CUipcMemHandle handle, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

326 return cydriver._cuIpcOpenMemHandle_v2(pdptr, handle, Flags) 

327  

328cdef CUresult cuIpcCloseMemHandle(CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil: 

329 return cydriver._cuIpcCloseMemHandle(dptr) 

330  

331cdef CUresult cuMemHostRegister(void* p, size_t bytesize, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

332 return cydriver._cuMemHostRegister_v2(p, bytesize, Flags) 2RpTw

333  

334cdef CUresult cuMemHostUnregister(void* p) except ?CUDA_ERROR_NOT_FOUND nogil: 

335 return cydriver._cuMemHostUnregister(p) 2RpTw

336  

337cdef CUresult cuMemcpy(CUdeviceptr dst, CUdeviceptr src, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

338 return cydriver._cuMemcpy(dst, src, ByteCount) 

339  

340cdef CUresult cuMemcpyPeer(CUdeviceptr dstDevice, CUcontext dstContext, CUdeviceptr srcDevice, CUcontext srcContext, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

341 return cydriver._cuMemcpyPeer(dstDevice, dstContext, srcDevice, srcContext, ByteCount) 

342  

343cdef CUresult cuMemcpyHtoD(CUdeviceptr dstDevice, const void* srcHost, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

344 return cydriver._cuMemcpyHtoD_v2(dstDevice, srcHost, ByteCount) 2+w[

345  

346cdef CUresult cuMemcpyDtoH(void* dstHost, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

347 return cydriver._cuMemcpyDtoH_v2(dstHost, srcDevice, ByteCount) 23 4 5 % +w[

348  

349cdef CUresult cuMemcpyDtoD(CUdeviceptr dstDevice, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

350 return cydriver._cuMemcpyDtoD_v2(dstDevice, srcDevice, ByteCount) 

351  

352cdef CUresult cuMemcpyDtoA(CUarray dstArray, size_t dstOffset, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

353 return cydriver._cuMemcpyDtoA_v2(dstArray, dstOffset, srcDevice, ByteCount) 

354  

355cdef CUresult cuMemcpyAtoD(CUdeviceptr dstDevice, CUarray srcArray, size_t srcOffset, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

356 return cydriver._cuMemcpyAtoD_v2(dstDevice, srcArray, srcOffset, ByteCount) 

357  

358cdef CUresult cuMemcpyHtoA(CUarray dstArray, size_t dstOffset, const void* srcHost, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

359 return cydriver._cuMemcpyHtoA_v2(dstArray, dstOffset, srcHost, ByteCount) 

360  

361cdef CUresult cuMemcpyAtoH(void* dstHost, CUarray srcArray, size_t srcOffset, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

362 return cydriver._cuMemcpyAtoH_v2(dstHost, srcArray, srcOffset, ByteCount) 

363  

364cdef CUresult cuMemcpyAtoA(CUarray dstArray, size_t dstOffset, CUarray srcArray, size_t srcOffset, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

365 return cydriver._cuMemcpyAtoA_v2(dstArray, dstOffset, srcArray, srcOffset, ByteCount) 

366  

367cdef CUresult cuMemcpy2D(const CUDA_MEMCPY2D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil: 

368 return cydriver._cuMemcpy2D_v2(pCopy) 

369  

370cdef CUresult cuMemcpy2DUnaligned(const CUDA_MEMCPY2D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil: 

371 return cydriver._cuMemcpy2DUnaligned_v2(pCopy) 

372  

373cdef CUresult cuMemcpy3D(const CUDA_MEMCPY3D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil: 

374 return cydriver._cuMemcpy3D_v2(pCopy) 

375  

376cdef CUresult cuMemcpy3DPeer(const CUDA_MEMCPY3D_PEER* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil: 

377 return cydriver._cuMemcpy3DPeer(pCopy) 

378  

379cdef CUresult cuMemcpyAsync(CUdeviceptr dst, CUdeviceptr src, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

380 return cydriver._cuMemcpyAsync(dst, src, ByteCount, hStream) 2w ( x y D ' E F O P Q Y # +fNiZg0g%f'fOiPi] ^ _ ` { | ybae2i.b)dGb} HbK

381  

382cdef CUresult cuMemcpyPeerAsync(CUdeviceptr dstDevice, CUcontext dstContext, CUdeviceptr srcDevice, CUcontext srcContext, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

383 return cydriver._cuMemcpyPeerAsync(dstDevice, dstContext, srcDevice, srcContext, ByteCount, hStream) 

384  

385cdef CUresult cuMemcpyHtoDAsync(CUdeviceptr dstDevice, const void* srcHost, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

386 return cydriver._cuMemcpyHtoDAsync_v2(dstDevice, srcHost, ByteCount, hStream) 

387  

388cdef CUresult cuMemcpyDtoHAsync(void* dstHost, CUdeviceptr srcDevice, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

389 return cydriver._cuMemcpyDtoHAsync_v2(dstHost, srcDevice, ByteCount, hStream) 2%d'd)f

390  

391cdef CUresult cuMemcpyDtoDAsync(CUdeviceptr dstDevice, CUdeviceptr srcDevice, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

392 return cydriver._cuMemcpyDtoDAsync_v2(dstDevice, srcDevice, ByteCount, hStream) 

393  

394cdef CUresult cuMemcpyHtoAAsync(CUarray dstArray, size_t dstOffset, const void* srcHost, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

395 return cydriver._cuMemcpyHtoAAsync_v2(dstArray, dstOffset, srcHost, ByteCount, hStream) 

396  

397cdef CUresult cuMemcpyAtoHAsync(void* dstHost, CUarray srcArray, size_t srcOffset, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

398 return cydriver._cuMemcpyAtoHAsync_v2(dstHost, srcArray, srcOffset, ByteCount, hStream) 

399  

400cdef CUresult cuMemcpy2DAsync(const CUDA_MEMCPY2D* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

401 return cydriver._cuMemcpy2DAsync_v2(pCopy, hStream) 

402  

403cdef CUresult cuMemcpy3DAsync(const CUDA_MEMCPY3D* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

404 return cydriver._cuMemcpy3DAsync_v2(pCopy, hStream) 

405  

406cdef CUresult cuMemcpy3DPeerAsync(const CUDA_MEMCPY3D_PEER* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

407 return cydriver._cuMemcpy3DPeerAsync(pCopy, hStream) 

408  

409cdef CUresult cuMemcpyBatchAsync(CUdeviceptr* dsts, CUdeviceptr* srcs, size_t* sizes, size_t count, CUmemcpyAttributes* attrs, size_t* attrsIdxs, size_t numAttrs, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

410 return cydriver._cuMemcpyBatchAsync_v2(dsts, srcs, sizes, count, attrs, attrsIdxs, numAttrs, hStream) 

411  

412cdef CUresult cuMemcpy3DBatchAsync(size_t numOps, CUDA_MEMCPY3D_BATCH_OP* opList, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

413 return cydriver._cuMemcpy3DBatchAsync_v2(numOps, opList, flags, hStream) 

414  

415cdef CUresult cuMemcpyWithAttributesAsync(CUdeviceptr dst, CUdeviceptr src, size_t size, CUmemcpyAttributes* attr, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

416 return cydriver._cuMemcpyWithAttributesAsync(dst, src, size, attr, hStream) 

417  

418cdef CUresult cuMemcpy3DWithAttributesAsync(CUDA_MEMCPY3D_BATCH_OP* op, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

419 return cydriver._cuMemcpy3DWithAttributesAsync(op, flags, hStream) 

420  

421cdef CUresult cuMemsetD8(CUdeviceptr dstDevice, unsigned char uc, size_t N) except ?CUDA_ERROR_NOT_FOUND nogil: 

422 return cydriver._cuMemsetD8_v2(dstDevice, uc, N) 

423  

424cdef CUresult cuMemsetD16(CUdeviceptr dstDevice, unsigned short us, size_t N) except ?CUDA_ERROR_NOT_FOUND nogil: 

425 return cydriver._cuMemsetD16_v2(dstDevice, us, N) 

426  

427cdef CUresult cuMemsetD32(CUdeviceptr dstDevice, unsigned int ui, size_t N) except ?CUDA_ERROR_NOT_FOUND nogil: 

428 return cydriver._cuMemsetD32_v2(dstDevice, ui, N) 

429  

430cdef CUresult cuMemsetD2D8(CUdeviceptr dstDevice, size_t dstPitch, unsigned char uc, size_t Width, size_t Height) except ?CUDA_ERROR_NOT_FOUND nogil: 

431 return cydriver._cuMemsetD2D8_v2(dstDevice, dstPitch, uc, Width, Height) 

432  

433cdef CUresult cuMemsetD2D16(CUdeviceptr dstDevice, size_t dstPitch, unsigned short us, size_t Width, size_t Height) except ?CUDA_ERROR_NOT_FOUND nogil: 

434 return cydriver._cuMemsetD2D16_v2(dstDevice, dstPitch, us, Width, Height) 

435  

436cdef CUresult cuMemsetD2D32(CUdeviceptr dstDevice, size_t dstPitch, unsigned int ui, size_t Width, size_t Height) except ?CUDA_ERROR_NOT_FOUND nogil: 

437 return cydriver._cuMemsetD2D32_v2(dstDevice, dstPitch, ui, Width, Height) 

438  

439cdef CUresult cuMemsetD8Async(CUdeviceptr dstDevice, unsigned char uc, size_t N, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

440 return cydriver._cuMemsetD8Async(dstDevice, uc, N, hStream) 2w ( x y #o'o)o*o+o=o?o_o|o~oapbpipjpoprptpupvpCpDp

441  

442cdef CUresult cuMemsetD16Async(CUdeviceptr dstDevice, unsigned short us, size_t N, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

443 return cydriver._cuMemsetD16Async(dstDevice, us, N, hStream) 2$o,o-o.o@o[o`ocpdpepkplpppwpxpypEpFp

444  

445cdef CUresult cuMemsetD32Async(CUdeviceptr dstDevice, unsigned int ui, size_t N, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

446 return cydriver._cuMemsetD32Async(dstDevice, ui, N, hStream) 2%o(o/o:o;o]o^o{o}ofpgphpmpnpqpspzpApBpGpHp

447  

448cdef CUresult cuMemsetD2D8Async(CUdeviceptr dstDevice, size_t dstPitch, unsigned char uc, size_t Width, size_t Height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

449 return cydriver._cuMemsetD2D8Async(dstDevice, dstPitch, uc, Width, Height, hStream) 

450  

451cdef CUresult cuMemsetD2D16Async(CUdeviceptr dstDevice, size_t dstPitch, unsigned short us, size_t Width, size_t Height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

452 return cydriver._cuMemsetD2D16Async(dstDevice, dstPitch, us, Width, Height, hStream) 

453  

454cdef CUresult cuMemsetD2D32Async(CUdeviceptr dstDevice, size_t dstPitch, unsigned int ui, size_t Width, size_t Height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

455 return cydriver._cuMemsetD2D32Async(dstDevice, dstPitch, ui, Width, Height, hStream) 

456  

457cdef CUresult cuArrayCreate(CUarray* pHandle, const CUDA_ARRAY_DESCRIPTOR* pAllocateArray) except ?CUDA_ERROR_NOT_FOUND nogil: 

458 return cydriver._cuArrayCreate_v2(pHandle, pAllocateArray) 2XW

459  

460cdef CUresult cuArrayGetDescriptor(CUDA_ARRAY_DESCRIPTOR* pArrayDescriptor, CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil: 

461 return cydriver._cuArrayGetDescriptor_v2(pArrayDescriptor, hArray) 

462  

463cdef CUresult cuArrayGetSparseProperties(CUDA_ARRAY_SPARSE_PROPERTIES* sparseProperties, CUarray array) except ?CUDA_ERROR_NOT_FOUND nogil: 

464 return cydriver._cuArrayGetSparseProperties(sparseProperties, array) 

465  

466cdef CUresult cuMipmappedArrayGetSparseProperties(CUDA_ARRAY_SPARSE_PROPERTIES* sparseProperties, CUmipmappedArray mipmap) except ?CUDA_ERROR_NOT_FOUND nogil: 

467 return cydriver._cuMipmappedArrayGetSparseProperties(sparseProperties, mipmap) 

468  

469cdef CUresult cuArrayGetMemoryRequirements(CUDA_ARRAY_MEMORY_REQUIREMENTS* memoryRequirements, CUarray array, CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil: 

470 return cydriver._cuArrayGetMemoryRequirements(memoryRequirements, array, device) 

471  

472cdef CUresult cuMipmappedArrayGetMemoryRequirements(CUDA_ARRAY_MEMORY_REQUIREMENTS* memoryRequirements, CUmipmappedArray mipmap, CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil: 

473 return cydriver._cuMipmappedArrayGetMemoryRequirements(memoryRequirements, mipmap, device) 

474  

475cdef CUresult cuArrayGetPlane(CUarray* pPlaneArray, CUarray hArray, unsigned int planeIdx) except ?CUDA_ERROR_NOT_FOUND nogil: 

476 return cydriver._cuArrayGetPlane(pPlaneArray, hArray, planeIdx) 

477  

478cdef CUresult cuArrayDestroy(CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil: 

479 return cydriver._cuArrayDestroy(hArray) 2XW

480  

481cdef CUresult cuArray3DCreate(CUarray* pHandle, const CUDA_ARRAY3D_DESCRIPTOR* pAllocateArray) except ?CUDA_ERROR_NOT_FOUND nogil: 

482 return cydriver._cuArray3DCreate_v2(pHandle, pAllocateArray) 

483  

484cdef CUresult cuArray3DGetDescriptor(CUDA_ARRAY3D_DESCRIPTOR* pArrayDescriptor, CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil: 

485 return cydriver._cuArray3DGetDescriptor_v2(pArrayDescriptor, hArray) 

486  

487cdef CUresult cuMipmappedArrayCreate(CUmipmappedArray* pHandle, const CUDA_ARRAY3D_DESCRIPTOR* pMipmappedArrayDesc, unsigned int numMipmapLevels) except ?CUDA_ERROR_NOT_FOUND nogil: 

488 return cydriver._cuMipmappedArrayCreate(pHandle, pMipmappedArrayDesc, numMipmapLevels) 

489  

490cdef CUresult cuMipmappedArrayGetLevel(CUarray* pLevelArray, CUmipmappedArray hMipmappedArray, unsigned int level) except ?CUDA_ERROR_NOT_FOUND nogil: 

491 return cydriver._cuMipmappedArrayGetLevel(pLevelArray, hMipmappedArray, level) 

492  

493cdef CUresult cuMipmappedArrayDestroy(CUmipmappedArray hMipmappedArray) except ?CUDA_ERROR_NOT_FOUND nogil: 

494 return cydriver._cuMipmappedArrayDestroy(hMipmappedArray) 

495  

496cdef CUresult cuMemGetHandleForAddressRange(void* handle, CUdeviceptr dptr, size_t size, CUmemRangeHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

497 return cydriver._cuMemGetHandleForAddressRange(handle, dptr, size, handleType, flags) 

498  

499cdef CUresult cuMemBatchDecompressAsync(CUmemDecompressParams* paramsArray, size_t count, unsigned int flags, size_t* errorIndex, CUstream stream) except ?CUDA_ERROR_NOT_FOUND nogil: 

500 return cydriver._cuMemBatchDecompressAsync(paramsArray, count, flags, errorIndex, stream) 

501  

502cdef CUresult cuMemAddressReserve(CUdeviceptr* ptr, size_t size, size_t alignment, CUdeviceptr addr, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

503 return cydriver._cuMemAddressReserve(ptr, size, alignment, addr, flags) 2]c^c'b_c

504  

505cdef CUresult cuMemAddressFree(CUdeviceptr ptr, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil: 

506 return cydriver._cuMemAddressFree(ptr, size) 2]c^c'b_c

507  

508cdef CUresult cuMemCreate(CUmemGenericAllocationHandle* handle, size_t size, const CUmemAllocationProp* prop, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

509 return cydriver._cuMemCreate(handle, size, prop, flags) 2]c^c'b_c

510  

511cdef CUresult cuMemRelease(CUmemGenericAllocationHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil: 

512 return cydriver._cuMemRelease(handle) 2]c^c'b_c

513  

514cdef CUresult cuMemMap(CUdeviceptr ptr, size_t size, size_t offset, CUmemGenericAllocationHandle handle, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

515 return cydriver._cuMemMap(ptr, size, offset, handle, flags) 2]c^c'b_c

516  

517cdef CUresult cuMemMapArrayAsync(CUarrayMapInfo* mapInfoList, unsigned int count, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

518 return cydriver._cuMemMapArrayAsync(mapInfoList, count, hStream) 

519  

520cdef CUresult cuMemUnmap(CUdeviceptr ptr, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil: 

521 return cydriver._cuMemUnmap(ptr, size) 2]c^c'b_c

522  

523cdef CUresult cuMemSetAccess(CUdeviceptr ptr, size_t size, const CUmemAccessDesc* desc, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil: 

524 return cydriver._cuMemSetAccess(ptr, size, desc, count) 2]c^c'b_c

525  

526cdef CUresult cuMemGetAccess(unsigned long long* flags, const CUmemLocation* location, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil: 

527 return cydriver._cuMemGetAccess(flags, location, ptr) 

528  

529cdef CUresult cuMemExportToShareableHandle(void* shareableHandle, CUmemGenericAllocationHandle handle, CUmemAllocationHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

530 return cydriver._cuMemExportToShareableHandle(shareableHandle, handle, handleType, flags) 

531  

532cdef CUresult cuMemImportFromShareableHandle(CUmemGenericAllocationHandle* handle, void* osHandle, CUmemAllocationHandleType shHandleType) except ?CUDA_ERROR_NOT_FOUND nogil: 

533 return cydriver._cuMemImportFromShareableHandle(handle, osHandle, shHandleType) 

534  

535cdef CUresult cuMemGetAllocationGranularity(size_t* granularity, const CUmemAllocationProp* prop, CUmemAllocationGranularity_flags option) except ?CUDA_ERROR_NOT_FOUND nogil: 

536 return cydriver._cuMemGetAllocationGranularity(granularity, prop, option) 2]c^c'b_c

537  

538cdef CUresult cuMemGetAllocationPropertiesFromHandle(CUmemAllocationProp* prop, CUmemGenericAllocationHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil: 

539 return cydriver._cuMemGetAllocationPropertiesFromHandle(prop, handle) 

540  

541cdef CUresult cuMemRetainAllocationHandle(CUmemGenericAllocationHandle* handle, void* addr) except ?CUDA_ERROR_NOT_FOUND nogil: 

542 return cydriver._cuMemRetainAllocationHandle(handle, addr) 2]c^c'b_c

543  

544cdef CUresult cuMemFreeAsync(CUdeviceptr dptr, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

545 return cydriver._cuMemFreeAsync(dptr, hStream) 27b8b9b}c~cadw ( x y D ' E F O P Q DbEbFb6 7 8 }d~dhd,w-w.w/w:w;w=w?w@w[w]w] ^ _ ` { | 1g2gGhWiXi8kbeGbKc5k} Yiid6kjd/bkd:bLcMcld;bmd=bndNcme}i3gZi7kHbIbneK fDwDzDbucudueuBqCqfuguhuiuju0Dku1Dlumu2Dnuoupu/DbEBu/u8FfvgvhvivFqGqjvkvlvmvnv}Fov~FpvqvaGrvsvtvuGKGFv?v/c:cgIyIQI8I?IhJzJRJSfNqTfOqUfVfWfPqQqXfYfRqSqTqZfUq0fVq1f2f3fWqXq4fYqZq0q1q5f2q6f7f8f9f!f#f3q4q$f1o

546  

547cdef CUresult cuMemAllocAsync(CUdeviceptr* dptr, size_t bytesize, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

548 return cydriver._cuMemAllocAsync(dptr, bytesize, hStream) 2}c~cadw x y D E F O P Q DbEbFb6 7 8

549  

550cdef CUresult cuMemPoolTrimTo(CUmemoryPool pool, size_t minBytesToKeep) except ?CUDA_ERROR_NOT_FOUND nogil: 

551 return cydriver._cuMemPoolTrimTo(pool, minBytesToKeep) 

552  

553cdef CUresult cuMemPoolSetAttribute(CUmemoryPool pool, CUmemPool_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil: 

554 return cydriver._cuMemPoolSetAttribute(pool, attr, value) 2^w5h

555  

556cdef CUresult cuMemPoolGetAttribute(CUmemoryPool pool, CUmemPool_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil: 

557 return cydriver._cuMemPoolGetAttribute(pool, attr, value) 27b8b9bw ( x y D ' E F ^w1g2gWiXi8kbeYiKhcejd/bLh,fMhdeNheeOhfekd:bPhge-fLc.f/f:f;fMc=fQhheld;bRhShThieUhjeVhkemd=bWhle?f@fXhndNcme3gK ~iejfjve9 wepdOcPcqd4hrdsdtdxeKb5hLbQc{f6hudvdlj!h)htgYj,e! -eNd5c6cOdbiPdQdRd.eSb4jTb7ccidiSdTd5j!jiiUggklkqkvkAkFkKkPkSfTfUfVfWfXfYfZf0f1f2f3f4f5f6f7f8f9f!f#f$f1o

558  

559cdef CUresult cuMemPoolSetAccess(CUmemoryPool pool, const CUmemAccessDesc* map, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil: 

560 return cydriver._cuMemPoolSetAccess(pool, map, count) 2iyjykylymyny}doy~dpyqyrysyhdtyuyvywyxyyyzyAyByCyDyEyFyGyHyIyJyKyLyMyNyOyPy] ^ _ ` { | GhGbKcHhIhJh} idKhcejd/bLh,fMhdeNheeOhfekd:bPhge-fLc.f/f:f;fMc=fQhheld;bRhShThieUhjeVhkemd=bWhle?f@fXhndNcme}iHbIbne.lZh0hK 4m5m6m7m/c:c

561  

562cdef CUresult cuMemPoolGetAccess(CUmemAccess_flags* flags, CUmemoryPool memPool, CUmemLocation* location) except ?CUDA_ERROR_NOT_FOUND nogil: 

563 return cydriver._cuMemPoolGetAccess(flags, memPool, location) 

564  

565cdef CUresult cuMemPoolCreate(CUmemoryPool* pool, const CUmemPoolProps* poolProps) except ?CUDA_ERROR_NOT_FOUND nogil: 

566 return cydriver._cuMemPoolCreate(pool, poolProps) 28JvwXo9JYoww!Jxw}d#J~dZo'ljq)lkq$Jyw%J*l'J(J)J*J+J,J-J.J/J:JzwAwBwCwlqDwEwFwGwHwIwJw;JKw+lmq=JLw?JMw,lnq%f'f@Jhh[JNw]JOw] ^ _ ` { | ^wGbKcHhIhJh} idKhcejd/bLh,fMhdeNheeOhfekd:bPhge-fLc.f/f:f;fMc=fQhheld;bRhShThieUhjeVhkemd=bWhle?f@fXhndNcme}iHbIbne.lZh0h4m5m6m7m/c:c

567  

568cdef CUresult cuMemPoolDestroy(CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil: 

569 return cydriver._cuMemPoolDestroy(pool) 2iyjykylymyny}doy~dpyqyrysyhdtyuyvywyxyyyzyAyByCyDyEyFyGyHyIyJyKyLyMyNyOyPy] ^ _ ` { | ^wGhGbKcHhIhJh} idKhcejd/bLh,fMhdeNheeOhfekd:bPhge-fLc.f/f:f;fMc=fQhheld;bRhShThieUhjeVhkemd=bWhle?f@fXhndNcme}iHbIbne.lZh0hK 4m5m6m7m/c:c

570  

571cdef CUresult cuMemGetDefaultMemPool(CUmemoryPool* pool_out, CUmemLocation* location, CUmemAllocationType typename) except ?CUDA_ERROR_NOT_FOUND nogil: 

572 return cydriver._cuMemGetDefaultMemPool(pool_out, location, typename) 

573  

574cdef CUresult cuMemGetMemPool(CUmemoryPool* pool, CUmemLocation* location, CUmemAllocationType typename) except ?CUDA_ERROR_NOT_FOUND nogil: 

575 return cydriver._cuMemGetMemPool(pool, location, typename) 24kKc`J5kZtHhIhJh0t} id6k-f7ALc8A.f9A/f!A:f#A;f$AMc%A=f'A@fNcZi7k

576  

577cdef CUresult cuMemSetMemPool(CUmemLocation* location, CUmemAllocationType typename, CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil: 

578 return cydriver._cuMemSetMemPool(location, typename, pool) 

579  

580cdef CUresult cuMemAllocFromPoolAsync(CUdeviceptr* dptr, size_t bytesize, CUmemoryPool pool, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

581 return cydriver._cuMemAllocFromPoolAsync(dptr, bytesize, pool, hStream) 27b8b9bw ( x y D ' E F XoYoLpPt}d~dY # (l}phd,w-w.w/w:w;w=w?w@w[w]wMpQtRtStNpTt+fNiZg0g%f'fOiPiUtVtOpWt] ^ _ ` { | 1g2gWiXi8kbeGbKc5k} Yiid6kjd/bkd:bLcMcld;bmd=bndNcme}i3gZi7kHbIbneK ~iejfjve9 wepdOcPcqd4hrdsdtdxeKb5hLbQc{f6hudvdlj!h)htgYj,e! -eNd5c6cOdbiPdQdRd.eSb4jTb7ccidiSdTd5j!jiiUg/c:cgklkqkvkAkFkKkPkSfNqTfOqUfVfWfPqQqXfYfRqSqTqZfUq0fVq1f2f3fWqXq4fYqZq0q1q5f2q6f7f8f9f!f#f3q4q$f1o

582  

583cdef CUresult cuMemPoolExportToShareableHandle(void* handle_out, CUmemoryPool pool, CUmemAllocationHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

584 return cydriver._cuMemPoolExportToShareableHandle(handle_out, pool, handleType, flags) 28JvwXo9JYoww!Jxw}d#J~dZo'ljq)lkq$Jyw%J*l'J(J)J*J+J,J-J.J/J:JzwAwBwCwlqDwEwFwGwHwIwJw;JKw+lmq=JLw?JMw,lnq%f'f@Jhh[JNw]JOw] ^ _ ` { | ce/b,fdeeefe:bgehe;bShiejeke=bleIbZh0h4m5m6m7m/c:c

585  

586cdef CUresult cuMemPoolImportFromShareableHandle(CUmemoryPool* pool_out, void* handle, CUmemAllocationHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

587 return cydriver._cuMemPoolImportFromShareableHandle(pool_out, handle, handleType, flags) 

588  

589cdef CUresult cuMemPoolExportPointer(CUmemPoolPtrExportData* shareData_out, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil: 

590 return cydriver._cuMemPoolExportPointer(shareData_out, ptr) 2XoYoLpPt}d~dY # (l}phd,w-w.w/w:w;w=w?w@w[w]wMpQtRtStNpTt+fNiZg0g%f'fOiPiUtVtOpWt] ^ _ ` { | Ib/c:c

591  

592cdef CUresult cuMemPoolImportPointer(CUdeviceptr* ptr_out, CUmemoryPool pool, CUmemPoolPtrExportData* shareData) except ?CUDA_ERROR_NOT_FOUND nogil: 

593 return cydriver._cuMemPoolImportPointer(ptr_out, pool, shareData) 

594  

595cdef CUresult cuMulticastCreate(CUmemGenericAllocationHandle* mcHandle, const CUmulticastObjectProp* prop) except ?CUDA_ERROR_NOT_FOUND nogil: 

596 return cydriver._cuMulticastCreate(mcHandle, prop) 

597  

598cdef CUresult cuMulticastAddDevice(CUmemGenericAllocationHandle mcHandle, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

599 return cydriver._cuMulticastAddDevice(mcHandle, dev) 

600  

601cdef CUresult cuMulticastBindMem(CUmemGenericAllocationHandle mcHandle, size_t mcOffset, CUmemGenericAllocationHandle memHandle, size_t memOffset, size_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

602 return cydriver._cuMulticastBindMem(mcHandle, mcOffset, memHandle, memOffset, size, flags) 

603  

604cdef CUresult cuMulticastBindMem_v2(CUmemGenericAllocationHandle mcHandle, CUdevice dev, size_t mcOffset, CUmemGenericAllocationHandle memHandle, size_t memOffset, size_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

605 return cydriver._cuMulticastBindMem_v2(mcHandle, dev, mcOffset, memHandle, memOffset, size, flags) 

606  

607cdef CUresult cuMulticastBindAddr(CUmemGenericAllocationHandle mcHandle, size_t mcOffset, CUdeviceptr memptr, size_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

608 return cydriver._cuMulticastBindAddr(mcHandle, mcOffset, memptr, size, flags) 

609  

610cdef CUresult cuMulticastBindAddr_v2(CUmemGenericAllocationHandle mcHandle, CUdevice dev, size_t mcOffset, CUdeviceptr memptr, size_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

611 return cydriver._cuMulticastBindAddr_v2(mcHandle, dev, mcOffset, memptr, size, flags) 

612  

613cdef CUresult cuMulticastUnbind(CUmemGenericAllocationHandle mcHandle, CUdevice dev, size_t mcOffset, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil: 

614 return cydriver._cuMulticastUnbind(mcHandle, dev, mcOffset, size) 

615  

616cdef CUresult cuMulticastGetGranularity(size_t* granularity, const CUmulticastObjectProp* prop, CUmulticastGranularity_flags option) except ?CUDA_ERROR_NOT_FOUND nogil: 

617 return cydriver._cuMulticastGetGranularity(granularity, prop, option) 

618  

619cdef CUresult cuPointerGetAttribute(void* data, CUpointer_attribute attribute, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil: 

620 return cydriver._cuPointerGetAttribute(data, attribute, ptr) 23 4 5 % ,d/d=d[d_d|dprpereueLbwdzeydDeCdFdUeTceb3e0 PbQbbcXcYcZc0cKdLd$e4c(e+eTbUd:e=e]eYd1djf!clbsf1 WbXbqc'c(c)c*c6dyfAf.cDfFfHfJfLfNfPfRf

621  

622cdef CUresult cuMemPrefetchAsync(CUdeviceptr devPtr, size_t count, CUmemLocation location, unsigned int flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

623 return cydriver._cuMemPrefetchAsync_v2(devPtr, count, location, flags, hStream) 

624  

625cdef CUresult cuMemAdvise(CUdeviceptr devPtr, size_t count, CUmem_advise advice, CUmemLocation location) except ?CUDA_ERROR_NOT_FOUND nogil: 

626 return cydriver._cuMemAdvise_v2(devPtr, count, advice, location) 20o

627  

628cdef CUresult cuMemPrefetchBatchAsync(CUdeviceptr* dptrs, size_t* sizes, size_t count, CUmemLocation* prefetchLocs, size_t* prefetchLocIdxs, size_t numPrefetchLocs, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

629 return cydriver._cuMemPrefetchBatchAsync(dptrs, sizes, count, prefetchLocs, prefetchLocIdxs, numPrefetchLocs, flags, hStream) 

630  

631cdef CUresult cuMemDiscardBatchAsync(CUdeviceptr* dptrs, size_t* sizes, size_t count, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

632 return cydriver._cuMemDiscardBatchAsync(dptrs, sizes, count, flags, hStream) 

633  

634cdef CUresult cuMemDiscardAndPrefetchBatchAsync(CUdeviceptr* dptrs, size_t* sizes, size_t count, CUmemLocation* prefetchLocs, size_t* prefetchLocIdxs, size_t numPrefetchLocs, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

635 return cydriver._cuMemDiscardAndPrefetchBatchAsync(dptrs, sizes, count, prefetchLocs, prefetchLocIdxs, numPrefetchLocs, flags, hStream) 

636  

637cdef CUresult cuMemRangeGetAttribute(void* data, size_t dataSize, CUmem_range_attribute attribute, CUdeviceptr devPtr, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil: 

638 return cydriver._cuMemRangeGetAttribute(data, dataSize, attribute, devPtr, count) 20o

639  

640cdef CUresult cuMemRangeGetAttributes(void** data, size_t* dataSizes, CUmem_range_attribute* attributes, size_t numAttributes, CUdeviceptr devPtr, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil: 

641 return cydriver._cuMemRangeGetAttributes(data, dataSizes, attributes, numAttributes, devPtr, count) 20o

642  

643cdef CUresult cuPointerSetAttribute(const void* value, CUpointer_attribute attribute, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil: 

644 return cydriver._cuPointerSetAttribute(value, attribute, ptr) 2pr

645  

646cdef CUresult cuPointerGetAttributes(unsigned int numAttributes, CUpointer_attribute* attributes, void** data, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil: 

647 return cydriver._cuPointerGetAttributes(numAttributes, attributes, data, ptr) 2R W c d e f g h i j k l m n o p q v r s t u G H I J M L z A B b DcC U V pr[Z%g'g(g)g*g+g,gGc-g.g/g:g;g=g?g@g[g]gHc^g_g`g{g|g}gIc~gahJcbhKq|iWiXi]ZPpRwQpSwRpTw4kKc3gZiK ^Z_Z`Z{Z|Z}Z~Za0b0

648  

649cdef CUresult cuStreamCreate(CUstream* phStream, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

650 return cydriver._cuStreamCreate(phStream, Flags) 2fh[ YW%d'dRiSiTi)fUiVi

651  

652cdef CUresult cuStreamCreateWithPriority(CUstream* phStream, unsigned int flags, int priority) except ?CUDA_ERROR_NOT_FOUND nogil: 

653 return cydriver._cuStreamCreateWithPriority(phStream, flags, priority) 2zbAb*fR S 4i2 W $ nbc d e f g h i j k l m n o p q v r s t u G H I J `c;c=c?c9dX !b{c|cobpbqbYbrb3 4 5 % Zb0b1bBc@c#b$bBbCbT ? @ %bM L z A B b 7b8b9b}c~cadw ( x y D ' E F O P Q DbEbFb6 7 8 C U V wb4b5b[c6bN Y # UkVkWkXkYkZk0k1k;k~JaK+fNiZg0g%f'fOiPi] ^ _ ` { | 5q6q7q8q9q!q0wEcZ Fc$k%k'k(k)k*kxb+k,k-k.k7i/kdhCc4g2o5g6g3o7g8g9g1i!g#g$g9kybae2i(d8i.b)d%q'q#o(q$o)q*q%o'o+q,q-q(o.q)o*o+o,o-o.o/o:o;o/q=o?o@o[o:q]o^o;q=q?q@q_o[q`o]q^q{o|o_q`q{q}o|q~oapbpcpdpepfpgphp}qipjpkplp~qmpnparbrcrdroperppfrgrqprphrirjrspkrtpupvpwpxpypzpApBplrCpDpEpFpmrGpHpnrorGb} 4oHbK 3iUsVsWs0p]htgfbWj2sug3pvgwgxg4p^h_h`h{h3c3s4c%eXj5p|h}h4s7syiUgmbfk#sVgXwWgXgYg)pziAiBiCi-c$s.cBf[n*pDiEi7d8d.p*s+s,s-s.s;s@s#q1w2w3w4w5w0i6w7w8w9w!w#w$w%w'w:k(wMq$q)weh*w

654  

655cdef CUresult cuStreamBeginCaptureToCig(CUstream hStream, CUstreamCigCaptureParams* streamCigCaptureParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

656 return cydriver._cuStreamBeginCaptureToCig(hStream, streamCigCaptureParams) 

657  

658cdef CUresult cuStreamEndCaptureToCig(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

659 return cydriver._cuStreamEndCaptureToCig(hStream) 

660  

661cdef CUresult cuStreamGetPriority(CUstream hStream, int* priority) except ?CUDA_ERROR_NOT_FOUND nogil: 

662 return cydriver._cuStreamGetPriority(hStream, priority) 

663  

664cdef CUresult cuStreamGetDevice(CUstream hStream, CUdevice* device) except ?CUDA_ERROR_NOT_FOUND nogil: 

665 return cydriver._cuStreamGetDevice(hStream, device) 

666  

667cdef CUresult cuStreamGetFlags(CUstream hStream, unsigned int* flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

668 return cydriver._cuStreamGetFlags(hStream, flags) 

669  

670cdef CUresult cuStreamGetId(CUstream hStream, unsigned long long* streamId) except ?CUDA_ERROR_NOT_FOUND nogil: 

671 return cydriver._cuStreamGetId(hStream, streamId) 

672  

673cdef CUresult cuStreamGetCtx(CUstream hStream, CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

674 return cydriver._cuStreamGetCtx(hStream, pctx) 2c d e f g h i j k l m n o p q v r s t u G H I J C N Y # UkVkWkXkYkZk0k1k5q6q7q8q9q!q.p#q0i

675  

676cdef CUresult cuStreamGetCtx_v2(CUstream hStream, CUcontext* pCtx, CUgreenCtx* pGreenCtx) except ?CUDA_ERROR_NOT_FOUND nogil: 

677 return cydriver._cuStreamGetCtx_v2(hStream, pCtx, pGreenCtx) 

678  

679cdef CUresult cuStreamWaitEvent(CUstream hStream, CUevent hEvent, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

680 return cydriver._cuStreamWaitEvent(hStream, hEvent, Flags) 2S 2 c d e f g h i j k l m n o p q v r s t u N eh

681  

682cdef CUresult cuStreamAddCallback(CUstream hStream, CUstreamCallback callback, void* userData, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

683 return cydriver._cuStreamAddCallback(hStream, callback, userData, flags) 

684  

685cdef CUresult cuStreamBeginCapture(CUstream hStream, CUstreamCaptureMode mode) except ?CUDA_ERROR_NOT_FOUND nogil: 

686 return cydriver._cuStreamBeginCapture_v2(hStream, mode) 2zbAb*fR S 4i2 W $ nbc d e f g h i j k l m n o p q v r s t u G H I J 7b8b9b}c~cadw x y D E F O P Q DbEbFb6 7 8 C U wb4b5b[c6bN

687  

688cdef CUresult cuStreamBeginCaptureToGraph(CUstream hStream, CUgraph hGraph, const CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, CUstreamCaptureMode mode) except ?CUDA_ERROR_NOT_FOUND nogil: 

689 return cydriver._cuStreamBeginCaptureToGraph(hStream, hGraph, dependencies, dependencyData, numDependencies, mode) 1cdefghijklmnopqvrstuGHIJCN

690  

691cdef CUresult cuThreadExchangeStreamCaptureMode(CUstreamCaptureMode* mode) except ?CUDA_ERROR_NOT_FOUND nogil: 

692 return cydriver._cuThreadExchangeStreamCaptureMode(mode) 

693  

694cdef CUresult cuStreamEndCapture(CUstream hStream, CUgraph* phGraph) except ?CUDA_ERROR_NOT_FOUND nogil: 

695 return cydriver._cuStreamEndCapture(hStream, phGraph) 2zbAb*fR S 4i2 W $ nbc d e f g h i j k l m n o p q v r s t u G H I J 7b8b9b}c~cadw x y D E F O P Q DbEbFb6 7 8 C U wb4b5b[c6bN

696  

697cdef CUresult cuStreamIsCapturing(CUstream hStream, CUstreamCaptureStatus* captureStatus) except ?CUDA_ERROR_NOT_FOUND nogil: 

698 return cydriver._cuStreamIsCapturing(hStream, captureStatus) 27b8b9b}c~cadw ( x y D ' E F O P Q DbEbFb6 7 8 XoYoLpPt}d~dY # (l}phd,w-w.w/w:w;w=w?w@w[w]wMpQtRtStNpTt+fNiZg0g%f'fOiPiUtVtOpWt] ^ _ ` { | 1g2gWiXi8kbeGbKc5k} Yiid6kjd/bkd:bLcMcld;bmd=bndNcme}i3gZi7kHbIbneK ~iejfjve9 wepdOcPcqd4hrdsdtdxeKb5hLbQc{f6hudvdlj!h)htgYj,e! -eNd5c6cOdbiPdQdRd.eSb4jTb7ccidiSdTd5j!jiiUg/c:cgklkqkvkAkFkKkPkSfNqTfOqUfVfWfPqQqXfYfRqSqTqZfUq0fVq1f2f3fWqXq4fYqZq0q1q5f2q6f7f8f9f!f#f3q4q$f1o

699  

700cdef CUresult cuStreamGetCaptureInfo(CUstream hStream, CUstreamCaptureStatus* captureStatus_out, cuuint64_t* id_out, CUgraph* graph_out, const CUgraphNode** dependencies_out, const CUgraphEdgeData** edgeData_out, size_t* numDependencies_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

701 return cydriver._cuStreamGetCaptureInfo_v3(hStream, captureStatus_out, id_out, graph_out, dependencies_out, edgeData_out, numDependencies_out) 2zbAb*fR S 4i2 W $ nbc d e f g h i j k l m n o p q v r s t u G H I J 7b8b9b}c~cadw x y D E F O P Q DbEbFb6 7 8 C U wb4b5b[c6bN

702  

703cdef CUresult cuStreamUpdateCaptureDependencies(CUstream hStream, CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

704 return cydriver._cuStreamUpdateCaptureDependencies_v2(hStream, dependencies, dependencyData, numDependencies, flags) 1RcdefghijklmnopqvrstuGHIJCN

705  

706cdef CUresult cuStreamAttachMemAsync(CUstream hStream, CUdeviceptr dptr, size_t length, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

707 return cydriver._cuStreamAttachMemAsync(hStream, dptr, length, flags) 

708  

709cdef CUresult cuStreamQuery(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

710 return cydriver._cuStreamQuery(hStream) 

711  

712cdef CUresult cuStreamSynchronize(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

713 return cydriver._cuStreamSynchronize(hStream) 2zbAbR S W $ nbc d e f g h i j k l m n o p q v r s t u G H I J `c;c=c?c9dX !b{c|cobpbqbYbrb3 4 5 % Zb0b1bBc@c#b$bBbCbT ? @ %bM L z A B b w ( x y D ' E F O P Q DbEbFb6 7 8 C U V [ EcFcyb%d'dRiSiTi)fUiVi(d8i%g'g(g)g*g+g,gGc-g.g/g:g;g=g?g@g[g]gHc^g_g`g{g|g}gIc~gahJcbhK $qeh

714  

715cdef CUresult cuStreamDestroy(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

716 return cydriver._cuStreamDestroy_v2(hStream) 2zbAb*fR S 4i2 W $ nbc d e f g h i j k l m n o p q v r s t u G H I J `c;c=c?c9dX !b{c|cobpbqbYbrb3 4 5 % Zb0b1bBc=k@c#b$bBbCbT ? @ %bM L z A B b 7b8b9b}c~cadw ( x y D ' E F O P Q DbEbFb6 7 8 C U V wb4b5b[c6bN ;k~JaKhd] ^ _ ` { | 5q6q7q8q9q!qfh[ 0wEcZ Fc$k%k'k(k)k*kxb+k,k-k.k7i/kdhCc4g5g6g3o7g8g9g!g#g$gGhybae2iYW%d'dRiSiTi)fUiVi(d8i.b)d%q'q#o(q$o)q*q%o'o+q,q-q(o.q)o*o+o,o-o.o/o:o;o/q=o?o@o[o:q]o^o;q=q?q@q_o[q`o]q^q{o|o_q`q{q}o|q~oapbpcpdpepfpgphp}qipjpkplp~qmpnparbrcrdroperppfrgrqprphrirjrspkrtpupvpwpxpypzpApBplrCpDpEpFpmrGpHpnrorGb} YhHbK 3itDxDNDpE.u/u:u;u2F=u?uDqEq@u[u]u^u_u3F`u4F{u|u5F}u~uav/FYG=v?v@v[vaI]v^vHqIq_v`v{v|v}vbI~vcIawbwdIcwdwew7d8duIMI4I/IdJvJNJ5J#q1w2w3w4w5w0i6w7w8w9w!w#w$w%w'w:k(wMq$q)weh*w

717  

718cdef CUresult cuStreamCopyAttributes(CUstream dst, CUstream src) except ?CUDA_ERROR_NOT_FOUND nogil: 

719 return cydriver._cuStreamCopyAttributes(dst, src) 

720  

721cdef CUresult cuStreamGetAttribute(CUstream hStream, CUstreamAttrID attr, CUstreamAttrValue* value_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

722 return cydriver._cuStreamGetAttribute(hStream, attr, value_out) 

723  

724cdef CUresult cuStreamSetAttribute(CUstream hStream, CUstreamAttrID attr, const CUstreamAttrValue* value) except ?CUDA_ERROR_NOT_FOUND nogil: 

725 return cydriver._cuStreamSetAttribute(hStream, attr, value) 

726  

727cdef CUresult cuEventCreate(CUevent* phEvent, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

728 return cydriver._cuEventCreate(phEvent, Flags) 2S 2 c d e f g h i j k l m n o p q v r s t u !b*d+d-d.d:d;d?d@d]d^d`d{dch#d5iBbCb$d6iT N Y # UkVkWkXkYkZk0k1k;k{JEcZ Fc|JPw}J$k%k'k(k)k*kxb+k,k-k.k7i/kdhCcZW3iSybjcjWyhjijseteOcPc~ ab}f~fnjojXs$h%hzdAdyj)hOb}m3y*hzjAj+h0sBjCjDjEjBd4yCdeg~m1sFjGj,h-hGeHeIeJe.hKeLeMeNeDdEdIjJjGdHdUcVcOjPjPbQb1c2c8e9eTjUj3pvgwg8y0j1j)e*e5c6cgbhbEgFg7j8j%y$j%jVdWd)jiiVb1n)yji*j+jki8s,j-j.j/jXd*yYdJg#p9s:j;jlimi`e{e|e}eni~eafbfcfZd0d?j@j2d3d#c$c`j{jWbXb+c,cSgTgckdkXwWgXg7d8d/yikjk=ynkok]ysktk{yxkykazCkDkezHkIkhzMkNkkzRkSk:keh

729  

730cdef CUresult cuEventRecord(CUevent hEvent, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

731 return cydriver._cuEventRecord(hEvent, hStream) 2S 2 c d e f g h i j k l m n o p q v r s t u N Y # UkVkWkXkYkZk0k1k;kEcZ Fc$k%k'k(k)k*kxb+k,k-k.k7i/kdhCc3i7d8d:keh

732  

733cdef CUresult cuEventRecordWithFlags(CUevent hEvent, CUstream hStream, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

734 return cydriver._cuEventRecordWithFlags(hEvent, hStream, flags) 

735  

736cdef CUresult cuEventQuery(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil: 

737 return cydriver._cuEventQuery(hEvent) 2ch#d$dxb7idh

738  

739cdef CUresult cuEventSynchronize(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil: 

740 return cydriver._cuEventSynchronize(hEvent) 2Z xbdhCc

741  

742cdef CUresult cuEventDestroy(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil: 

743 return cydriver._cuEventDestroy_v2(hEvent) 2S 2 c d e f g h i j k l m n o p q v r s t u ,t-t.t/t:t;t=t?t@t[t]t^t_tch#d5i$d6iN ;khd{JEcZ Fc|JPw}J$k%k'k(k)k*kxb+k,k-k.k7i/kdhCcZW3ijD`t{tDD|t}t~tauBqCqqurusutuuuvufEwuxuyuzuAuBuCuDuDEEuFuGuHuIuJuKuLuEEMuFENuOuGEPuQuRuSuTuUuVuWuXuYuZu0u1u2u3u4u5u6u7u8u9u!u#u$u%u'u(u)u*u+u,u-u?uDqEq$FbvcvdvevFqGquvvvwvxvyvzvOGAvBvCvDvEvFvGvHv$GIvJvKvLvMvNvOvPv%GQv'GRvSv(GTvUvVvWvXvYvZv0v1v2v3v4v5v6v7v8v9v!v#v$v%v'v(v)v*v+v,v-v.v/v:v;v^vHqIq7d8dkIfwgwCIhwiwUIjwkw$Ilwmw^InwowlJpwqwDJrwswVJtwuw:keh

744  

745cdef CUresult cuEventElapsedTime(float* pMilliseconds, CUevent hStart, CUevent hEnd) except ?CUDA_ERROR_NOT_FOUND nogil: 

746 return cydriver._cuEventElapsedTime_v2(pMilliseconds, hStart, hEnd) 2EcZ FcCc

747  

748cdef CUresult cuImportExternalMemory(CUexternalMemory* extMem_out, const CUDA_EXTERNAL_MEMORY_HANDLE_DESC* memHandleDesc) except ?CUDA_ERROR_NOT_FOUND nogil: 

749 return cydriver._cuImportExternalMemory(extMem_out, memHandleDesc) 

750  

751cdef CUresult cuExternalMemoryGetMappedBuffer(CUdeviceptr* devPtr, CUexternalMemory extMem, const CUDA_EXTERNAL_MEMORY_BUFFER_DESC* bufferDesc) except ?CUDA_ERROR_NOT_FOUND nogil: 

752 return cydriver._cuExternalMemoryGetMappedBuffer(devPtr, extMem, bufferDesc) 

753  

754cdef CUresult cuExternalMemoryGetMappedMipmappedArray(CUmipmappedArray* mipmap, CUexternalMemory extMem, const CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC* mipmapDesc) except ?CUDA_ERROR_NOT_FOUND nogil: 

755 return cydriver._cuExternalMemoryGetMappedMipmappedArray(mipmap, extMem, mipmapDesc) 

756  

757cdef CUresult cuDestroyExternalMemory(CUexternalMemory extMem) except ?CUDA_ERROR_NOT_FOUND nogil: 

758 return cydriver._cuDestroyExternalMemory(extMem) 

759  

760cdef CUresult cuImportExternalSemaphore(CUexternalSemaphore* extSem_out, const CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC* semHandleDesc) except ?CUDA_ERROR_NOT_FOUND nogil: 

761 return cydriver._cuImportExternalSemaphore(extSem_out, semHandleDesc) 

762  

763cdef CUresult cuSignalExternalSemaphoresAsync(const CUexternalSemaphore* extSemArray, const CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS* paramsArray, unsigned int numExtSems, CUstream stream) except ?CUDA_ERROR_NOT_FOUND nogil: 

764 return cydriver._cuSignalExternalSemaphoresAsync(extSemArray, paramsArray, numExtSems, stream) 

765  

766cdef CUresult cuWaitExternalSemaphoresAsync(const CUexternalSemaphore* extSemArray, const CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS* paramsArray, unsigned int numExtSems, CUstream stream) except ?CUDA_ERROR_NOT_FOUND nogil: 

767 return cydriver._cuWaitExternalSemaphoresAsync(extSemArray, paramsArray, numExtSems, stream) 

768  

769cdef CUresult cuDestroyExternalSemaphore(CUexternalSemaphore extSem) except ?CUDA_ERROR_NOT_FOUND nogil: 

770 return cydriver._cuDestroyExternalSemaphore(extSem) 

771  

772cdef CUresult cuStreamWaitValue32(CUstream stream, CUdeviceptr addr, cuuint32_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

773 return cydriver._cuStreamWaitValue32_v2(stream, addr, value, flags) 

774  

775cdef CUresult cuStreamWaitValue64(CUstream stream, CUdeviceptr addr, cuuint64_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

776 return cydriver._cuStreamWaitValue64_v2(stream, addr, value, flags) 

777  

778cdef CUresult cuStreamWriteValue32(CUstream stream, CUdeviceptr addr, cuuint32_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

779 return cydriver._cuStreamWriteValue32_v2(stream, addr, value, flags) 

780  

781cdef CUresult cuStreamWriteValue64(CUstream stream, CUdeviceptr addr, cuuint64_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

782 return cydriver._cuStreamWriteValue64_v2(stream, addr, value, flags) 

783  

784cdef CUresult cuStreamBatchMemOp(CUstream stream, unsigned int count, CUstreamBatchMemOpParams* paramArray, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

785 return cydriver._cuStreamBatchMemOp_v2(stream, count, paramArray, flags) 

786  

787cdef CUresult cuFuncGetAttribute(int* pi, CUfunction_attribute attrib, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil: 

788 return cydriver._cuFuncGetAttribute(pi, attrib, hfunc) 

789  

790cdef CUresult cuFuncSetAttribute(CUfunction hfunc, CUfunction_attribute attrib, int value) except ?CUDA_ERROR_NOT_FOUND nogil: 

791 return cydriver._cuFuncSetAttribute(hfunc, attrib, value) 

792  

793cdef CUresult cuFuncSetCacheConfig(CUfunction hfunc, CUfunc_cache config) except ?CUDA_ERROR_NOT_FOUND nogil: 

794 return cydriver._cuFuncSetCacheConfig(hfunc, config) 

795  

796cdef CUresult cuFuncGetModule(CUmodule* hmod, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil: 

797 return cydriver._cuFuncGetModule(hmod, hfunc) 

798  

799cdef CUresult cuFuncGetName(const char** name, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil: 

800 return cydriver._cuFuncGetName(name, hfunc) 2c0

801  

802cdef CUresult cuFuncGetParamInfo(CUfunction func, size_t paramIndex, size_t* paramOffset, size_t* paramSize) except ?CUDA_ERROR_NOT_FOUND nogil: 

803 return cydriver._cuFuncGetParamInfo(func, paramIndex, paramOffset, paramSize) 

804  

805cdef CUresult cuFuncGetParamCount(CUfunction func, size_t* paramCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

806 return cydriver._cuFuncGetParamCount(func, paramCount) 

807  

808cdef CUresult cuFuncIsLoaded(CUfunctionLoadingState* state, CUfunction function) except ?CUDA_ERROR_NOT_FOUND nogil: 

809 return cydriver._cuFuncIsLoaded(state, function) 

810  

811cdef CUresult cuFuncLoad(CUfunction function) except ?CUDA_ERROR_NOT_FOUND nogil: 

812 return cydriver._cuFuncLoad(function) 

813  

814cdef CUresult cuLaunchKernel(CUfunction f, unsigned int gridDimX, unsigned int gridDimY, unsigned int gridDimZ, unsigned int blockDimX, unsigned int blockDimY, unsigned int blockDimZ, unsigned int sharedMemBytes, CUstream hStream, void** kernelParams, void** extra) except ?CUDA_ERROR_NOT_FOUND nogil: 

815 return cydriver._cuLaunchKernel(f, gridDimX, gridDimY, gridDimZ, blockDimX, blockDimY, blockDimZ, sharedMemBytes, hStream, kernelParams, extra) 2%d'dRiSiTi)fUiVi

816  

817cdef CUresult cuLaunchKernelEx(const CUlaunchConfig* config, CUfunction f, void** kernelParams, void** extra) except ?CUDA_ERROR_NOT_FOUND nogil: 

818 return cydriver._cuLaunchKernelEx(config, f, kernelParams, extra) 2R S 2 W $ nbc d e f g h i j k l m n o p q v r s t u G H I J w ( x y D ' E F O P Q C U wb4b5b[c6bN Y # Z xbCcyb(d8i%g'g(g)g*g+g,gGc-g.g/g:g;g=g?g@g[g]gHc^g_g`g{g|g}gIc~gahJcbhK

819  

820cdef CUresult cuLaunchCooperativeKernel(CUfunction f, unsigned int gridDimX, unsigned int gridDimY, unsigned int gridDimZ, unsigned int blockDimX, unsigned int blockDimY, unsigned int blockDimZ, unsigned int sharedMemBytes, CUstream hStream, void** kernelParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

821 return cydriver._cuLaunchCooperativeKernel(f, gridDimX, gridDimY, gridDimZ, blockDimX, blockDimY, blockDimZ, sharedMemBytes, hStream, kernelParams) 

822  

823cdef CUresult cuLaunchCooperativeKernelMultiDevice(CUDA_LAUNCH_PARAMS* launchParamsList, unsigned int numDevices, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

824 return cydriver._cuLaunchCooperativeKernelMultiDevice(launchParamsList, numDevices, flags) 

825  

826cdef CUresult cuLaunchHostFunc(CUstream hStream, CUhostFn fn, void* userData) except ?CUDA_ERROR_NOT_FOUND nogil: 

827 return cydriver._cuLaunchHostFunc(hStream, fn, userData) 2zbAb

828  

829cdef CUresult cuLaunchHostFunc_v2(CUstream hStream, CUhostFn fn, void* userData, unsigned int syncMode) except ?CUDA_ERROR_NOT_FOUND nogil: 

830 return cydriver._cuLaunchHostFunc_v2(hStream, fn, userData, syncMode) 

831  

832cdef CUresult cuFuncSetBlockShape(CUfunction hfunc, int x, int y, int z) except ?CUDA_ERROR_NOT_FOUND nogil: 

833 return cydriver._cuFuncSetBlockShape(hfunc, x, y, z) 

834  

835cdef CUresult cuFuncSetSharedSize(CUfunction hfunc, unsigned int numbytes) except ?CUDA_ERROR_NOT_FOUND nogil: 

836 return cydriver._cuFuncSetSharedSize(hfunc, numbytes) 

837  

838cdef CUresult cuParamSetSize(CUfunction hfunc, unsigned int numbytes) except ?CUDA_ERROR_NOT_FOUND nogil: 

839 return cydriver._cuParamSetSize(hfunc, numbytes) 

840  

841cdef CUresult cuParamSeti(CUfunction hfunc, int offset, unsigned int value) except ?CUDA_ERROR_NOT_FOUND nogil: 

842 return cydriver._cuParamSeti(hfunc, offset, value) 

843  

844cdef CUresult cuParamSetf(CUfunction hfunc, int offset, float value) except ?CUDA_ERROR_NOT_FOUND nogil: 

845 return cydriver._cuParamSetf(hfunc, offset, value) 

846  

847cdef CUresult cuParamSetv(CUfunction hfunc, int offset, void* ptr, unsigned int numbytes) except ?CUDA_ERROR_NOT_FOUND nogil: 

848 return cydriver._cuParamSetv(hfunc, offset, ptr, numbytes) 

849  

850cdef CUresult cuLaunch(CUfunction f) except ?CUDA_ERROR_NOT_FOUND nogil: 

851 return cydriver._cuLaunch(f) 

852  

853cdef CUresult cuLaunchGrid(CUfunction f, int grid_width, int grid_height) except ?CUDA_ERROR_NOT_FOUND nogil: 

854 return cydriver._cuLaunchGrid(f, grid_width, grid_height) 

855  

856cdef CUresult cuLaunchGridAsync(CUfunction f, int grid_width, int grid_height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

857 return cydriver._cuLaunchGridAsync(f, grid_width, grid_height, hStream) 

858  

859cdef CUresult cuParamSetTexRef(CUfunction hfunc, int texunit, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

860 return cydriver._cuParamSetTexRef(hfunc, texunit, hTexRef) 

861  

862cdef CUresult cuFuncSetSharedMemConfig(CUfunction hfunc, CUsharedconfig config) except ?CUDA_ERROR_NOT_FOUND nogil: 

863 return cydriver._cuFuncSetSharedMemConfig(hfunc, config) 

864  

865cdef CUresult cuGraphCreate(CUgraph* phGraph, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

866 return cydriver._cuGraphCreate(phGraph, flags) 2VxWxXxYxZx0xyV1x2x`k!i{k3x#i|k}k4x5x6x7x8x9i9x!x#x$xX %x'x(x)x*x+x,x-x.x/x:x;x=x?x@x[x]x^x_x`x{x|x}x~xaybycydyeyfygy~kal(b$i*d+d%iblcldlelbd,dihjhkhlhflglhlil)b'i-d.d(ijlklllmlcd/dmhnhohphnlolpl)iqlhy*irlsltl+iul,ivlwlxlyl*b-i:d;d.izlAlBlCldd=dqhrhshthDlElFlGl+b/i?d@d:iHlIlJlKled[duhvhwhxhJqLlMlNl,b;i]d^d=iOlPlQlRlfd_dyhzhAhBhSlTlUlVl-b?i`d{d@iWlXlYlZlgd|dChDhEhFh0l1l2l[i3l]i4l5l6l^i7l_i8l9l=k!l`i#l{i$l%l[k0W1W2W3WZw4W_wsr3khq!d]k@c6o7o8o9osbtbubvb#b$b2bch#d5iBbCb$d6i(fT ? @ 3b%b!oM L z A B bKIp?k@kb ^kDc_kV cKfh[ `wdK5W8m?bTpajbjcjdjTyLq9m!moepe1hUy$m%m(m@bVpgjhjijjjXy)m*m+mqere2hYy-m.mJbsetekj[f]f^fodue3h_f`fve9 wepdOcPcqd4hrdsdtdKbLbQc6hudvd~ abMb) * + , 7hbb|f}f~fag8h/m:mRcwdbgXp;m=m?m[bYpmjnjojpjZy@m[m]myeze9h0y_m`mqjNb{m#h$h%h'hYsrjsjtjxdydcgZsvjwjxjcbzdAd(hAeBeCeScDedgEeFeyjOb}m*hzjAj+h0sBjCjDjBdCdeg1sFjGj,h-hGeHeIeJe.hKeLeMeNedbDdEdOePeQeFdfgReSean]b1pHjIjJjKjbncndnTeUe/h5yenfngghgigjggnhninjnkn:h^bkglgGdHdmgLjVeWeXeYeTcZeMj0e1e_bUcVcWcId`b{beb|b}b~blnacWwNjOjPjQj6ymnnnon2e3e;h7yqnrn0 PbQbbcXcYcZc0c- 1c2cJd4e5eKd6e7eRjcc=h?h8e9e@hsnngogpg!eLdqgunrgsgvndcSjTjUjVjwnxnyn#e$e[hznAn]hfbWjugvgwgxg4p^h_h`h3c4c%e5p|h}hBnCnec6pZj0j1j2j9yDnEnFn'e(e~h!yHnInRb)e*e3jygzgAgMd+eaiBgCg,e! -eNd5c6cOdbiPdQdRdSbTb7cdiSdTdgbhbUb. / : ; 5oibDgEgFgGgeiJnKn8cUdHg8pLnMnNnfc9p6j7j8j9j#yOnPnQn/e:efi$ySnTnUngc!p#j$j%j'j'yVnWnXn;e=egi(yZn0n(jjbVdWdhi?e@e[e9c]eIg^e_e)jVb1nji*j+jki8s,j-j.jXdYdJg9s:j;jlimi`e{e|e}eni~eafbfcfkbZd0ddfefff1dKggfhf2nhc$p=j?j@j[j3n4n5nifjfoi+y6n7nLgMgNgOg8n9n!n#n$npiicPgQg2d3dRg]jkflfmfnf!cof^jpfqfjc#c$c%c4dkclclbmcncoc%npc%p_j`j{j|j,y'n(n)nrfsfqi-y+n,n1 WbXbqc'c(c)c*c= +c,c5dtfuf6dvfwf-nrc}j~jSgTgak'prisitixfyfui(pviwi/nscbkckdkek:n;n=nzfAfxi?n@nyimbfkVgWgXgYg)pziAiBi-c.cBf*pDiEi]n^ntc+phkikjkkk:y_n`n{nCfDfFi;y}n~naouc/pmknkokpk?ybocodoEfFfGi@yfogohovc;prksktkuk^yiojokoGfHfHi_ymonooowc?pwkxkykzk|ypoqoroIfJfIi}ytouovoxc[pBkCkDkEkbzwoxoyoKfLfJiczAoBoCoyc^pGkHkIkJkfzDoEoFoMfNfKigzHoIoJozc`pLkMkNkOkizKoLoMoOfPfLijzOoPoQoAc{pQkRkSkTklzRoSoToQfRfMimzVoWo

867  

868cdef CUresult cuGraphAddKernelNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

869 return cydriver._cuGraphAddKernelNode_v2(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 2X obpbqbYbrbQi2k(bbd)bcd*bdd+bed,bfd-bgd!dsbtbubvb2b(fT ? @ 3bM L z A B b V ?boe@bqeJbod9 Kb~ abMb) * + , bbRc[byeNbxdcbScObBddb]bTe^bYe_bUcVcWcId`b{beb|b}b~bac2e0 - cc!edc#efb3cec'eRbMd! SbgbhbUb. / : ; ib8cfc/egc;ejb9cVbXdkbhcificnfjc#c$c%c4dkclclbmcncocpcrf1 = rcxfsczfmb-ctcCfucEfvcGfwcIfxcKfycMfzcOfAcQf

870  

871cdef CUresult cuGraphKernelNodeGetParams(CUgraphNode hNode, CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

872 return cydriver._cuGraphKernelNodeGetParams_v2(hNode, nodeParams) 2eKsbtbubvb2b3bb

873  

874cdef CUresult cuGraphKernelNodeSetParams(CUgraphNode hNode, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

875 return cydriver._cuGraphKernelNodeSetParams_v2(hNode, nodeParams) 

876  

877cdef CUresult cuGraphAddMemcpyNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_MEMCPY3D* copyParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

878 return cydriver._cuGraphAddMemcpyNode(phGraphNode, hGraph, dependencies, numDependencies, copyParams, ctx) 23 4 5 % ,d/d=d[d_d|dpereueLbwdzeydDeCdFdUeTceb3e0 PbQbbcXcYcZc0cKdLd$e4c(e+eTbUd:e=e]eYd1djf!clbsf1 WbXbqc'c(c)c*c6dyfAf.cDfFfHfJfLfNfPfRf

879  

880cdef CUresult cuGraphMemcpyNodeGetParams(CUgraphNode hNode, CUDA_MEMCPY3D* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

881 return cydriver._cuGraphMemcpyNodeGetParams(hNode, nodeParams) 1[

882  

883cdef CUresult cuGraphMemcpyNodeSetParams(CUgraphNode hNode, const CUDA_MEMCPY3D* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

884 return cydriver._cuGraphMemcpyNodeSetParams(hNode, nodeParams) 

885  

886cdef CUresult cuGraphAddMemsetNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_MEMSET_NODE_PARAMS* memsetParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

887 return cydriver._cuGraphAddMemsetNode(phGraphNode, hGraph, dependencies, numDependencies, memsetParams, ctx) 23 4 5 % Zb0b1bBcihjhkhlhmhnhohphqhrhshthuhvhwhxhyhzhAhBhChDhEhFhb Dc1h2h3hQcbg9hcgdgegfg/hZe|b;h- 1c2cJd4e5eKd6e7eqg[h%e~hai7cHgfigiIgJgKgoiofmcqi= +c,c5dtfuf6dvfwfuixiBfFiGiHiIiJiKiLiMi

888  

889cdef CUresult cuGraphMemsetNodeGetParams(CUgraphNode hNode, CUDA_MEMSET_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

890 return cydriver._cuGraphMemsetNodeGetParams(hNode, nodeParams) 1b

891  

892cdef CUresult cuGraphMemsetNodeSetParams(CUgraphNode hNode, const CUDA_MEMSET_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

893 return cydriver._cuGraphMemsetNodeSetParams(hNode, nodeParams) 

894  

895cdef CUresult cuGraphAddHostNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

896 return cydriver._cuGraphAddHostNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 2`c{c|cblcljlklzlAlHlIlOlPlWlXl#b$b%bLq)m[frdMb8h@mrjAeBj-h.hOebngghgigjgVeIdmnbcJdngwn^hDnygPdUbeiOnVn?e,jminidf3nLgMgNgOgkf4d'nqc5dri:nzi_nboiopowoDoKoRo

897  

898cdef CUresult cuGraphHostNodeGetParams(CUgraphNode hNode, CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

899 return cydriver._cuGraphHostNodeGetParams(hNode, nodeParams) 

900  

901cdef CUresult cuGraphHostNodeSetParams(CUgraphNode hNode, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

902 return cydriver._cuGraphHostNodeSetParams(hNode, nodeParams) 

903  

904cdef CUresult cuGraphAddChildGraphNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUgraph childGraph) except ?CUDA_ERROR_NOT_FOUND nogil: 

905 return cydriver._cuGraphAddChildGraphNode(phGraphNode, hGraph, dependencies, numDependencies, childGraph) 2R X (b)b*b+b,b-b2b3b?b@bJb9 ~ abMb) * + , bb[bNbcbObdb]b^b_bac0 - ccdcfbecRb! gbhbUb. / : ; ibfcgcjbVbkbhcicjcpc1 = rcscmbtcucvcwcxcyczcAc

906  

907cdef CUresult cuGraphChildGraphNodeGetGraph(CUgraphNode hNode, CUgraph* phGraph) except ?CUDA_ERROR_NOT_FOUND nogil: 

908 return cydriver._cuGraphChildGraphNodeGetGraph(hNode, phGraph) 2X (b)b*b+b,b-b2b3b?b@bJb9 ~ abMb) * + , bb[bNbcbObdb]b^b_bac0 - ccdcfbecRb! gbhbUb. / : ; ibfcgcjbVbkbhcicjcpc1 = rcscmbtcucvcwcxcyczcAc

909  

910cdef CUresult cuGraphAddEmptyNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil: 

911 return cydriver._cuGraphAddEmptyNode(phGraphNode, hGraph, dependencies, numDependencies) 2!i#i9i3 4 5 % eqfqgq$i,d'i/d)i*i+i,i-i=d/i[d;i_d?i|d[i]i^i_i=k`i{i_w3kM L z A B bKIp?k@k^k_k`wdKajpegjreuepdLb|fwdmjze#hydxjcbzdAd(hAeBeCeScDedgEeFe*hCdFdHjUelgTcebNj3e0 PbQbbcXcYcZc0cKd?hLdSj$eug4cZj(e+eNdTbDgUd6j:e#j=e(jjbVdWdhi?e@e[e9c]eIg^e_ejiYd1d=jjfQg!clb_jsf1 WbXbqc'c(c)c*c6d~jyfbkAfVg.chkDfmkFfrkHfwkJfBkLfGkNfLkPfQkRf

912  

913cdef CUresult cuGraphAddEventRecordNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil: 

914 return cydriver._cuGraphAddEventRecordNode(phGraphNode, hGraph, dependencies, numDependencies, event) 2!b*d-d:d?d]d`dch#d5iBbCbT bjhjseOc~ }fnj$hzdzj,h-hGeHeIeJeDdIjGdUcOjPb1c8eTjvg0j)e5cgbEg7j$jVd*jlimi`e{e|e}eZd?j2d#c`jWb+cSgckWgiknkskxkCkHkMkRk

915  

916cdef CUresult cuGraphEventRecordNodeGetEvent(CUgraphNode hNode, CUevent* event_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

917 return cydriver._cuGraphEventRecordNodeGetEvent(hNode, event_out) 

918  

919cdef CUresult cuGraphEventRecordNodeSetEvent(CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil: 

920 return cydriver._cuGraphEventRecordNodeSetEvent(hNode, event) 

921  

922cdef CUresult cuGraphAddEventWaitNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil: 

923 return cydriver._cuGraphAddEventWaitNode(phGraphNode, hGraph, dependencies, numDependencies, event) 2!b+d.d;d@d^d{dBbCb$d6icjijtePcab~foj%hAdAj,h.hKeLeMeNeEdJjHdVcPjQb2c9eUjwg1j*e6chbFg8j%jWd+jlini~eafbfcf0d@j3d$c{jXb,cTgdkXgjkoktkykDkIkNkSk

924  

925cdef CUresult cuGraphEventWaitNodeGetEvent(CUgraphNode hNode, CUevent* event_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

926 return cydriver._cuGraphEventWaitNodeGetEvent(hNode, event_out) 

927  

928cdef CUresult cuGraphEventWaitNodeSetEvent(CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil: 

929 return cydriver._cuGraphEventWaitNodeSetEvent(hNode, event) 

930  

931cdef CUresult cuGraphAddExternalSemaphoresSignalNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

932 return cydriver._cuGraphAddExternalSemaphoresSignalNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 

933  

934cdef CUresult cuGraphExternalSemaphoresSignalNodeGetParams(CUgraphNode hNode, CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* params_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

935 return cydriver._cuGraphExternalSemaphoresSignalNodeGetParams(hNode, params_out) 

936  

937cdef CUresult cuGraphExternalSemaphoresSignalNodeSetParams(CUgraphNode hNode, const CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

938 return cydriver._cuGraphExternalSemaphoresSignalNodeSetParams(hNode, nodeParams) 

939  

940cdef CUresult cuGraphAddExternalSemaphoresWaitNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_EXT_SEM_WAIT_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

941 return cydriver._cuGraphAddExternalSemaphoresWaitNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 

942  

943cdef CUresult cuGraphExternalSemaphoresWaitNodeGetParams(CUgraphNode hNode, CUDA_EXT_SEM_WAIT_NODE_PARAMS* params_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

944 return cydriver._cuGraphExternalSemaphoresWaitNodeGetParams(hNode, params_out) 

945  

946cdef CUresult cuGraphExternalSemaphoresWaitNodeSetParams(CUgraphNode hNode, const CUDA_EXT_SEM_WAIT_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

947 return cydriver._cuGraphExternalSemaphoresWaitNodeSetParams(hNode, nodeParams) 

948  

949cdef CUresult cuGraphAddBatchMemOpNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

950 return cydriver._cuGraphAddBatchMemOpNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 

951  

952cdef CUresult cuGraphBatchMemOpNodeGetParams(CUgraphNode hNode, CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

953 return cydriver._cuGraphBatchMemOpNodeGetParams(hNode, nodeParams_out) 

954  

955cdef CUresult cuGraphBatchMemOpNodeSetParams(CUgraphNode hNode, const CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

956 return cydriver._cuGraphBatchMemOpNodeSetParams(hNode, nodeParams) 

957  

958cdef CUresult cuGraphExecBatchMemOpNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

959 return cydriver._cuGraphExecBatchMemOpNodeSetParams(hGraphExec, hNode, nodeParams) 

960  

961cdef CUresult cuGraphAddMemAllocNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUDA_MEM_ALLOC_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

962 return cydriver._cuGraphAddMemAllocNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 2qzrz~prrXtszYt`k!i{k#i|k}kaq;c=c?c9d3 4 5 % Zb0b1bBcbqcqdqeqfqgq~kal$i*d+d%ibd,dihjhkhlhhlil'i-d.d(icd/dmhnhohphpl)iql*irlsltl+iul,ivlwlxlyl-i:d;d.idd=dqhrhshthFlGl/i?d@d:ied[duhvhwhxhMlNl;i]d^d=ifd_dyhzhAhBhUlVl?i`d{d@igd|dChDhEhFh2l[i3l]i4l5l6l^i7l_i8l9l!l`i#l{i$l%l3khq@c#d$dfh8majdjpe1h(mgjjjre2hJbsetekj[f]f^fodue3h_f`fvepdqdLbQc7h|fagwdbg?mmjpjze9hqj#h'hydcgxjcbzdAd(hAeBeCeScDedgEeFeyj*h+hCdegdbDdEdOePeQeFdfgReSeanHjKjUe/h:hlgmgTcZeWceb|blnNjQj3e;h0 PbQbbcXcYcZc0c- 1c2cJd4e5eKd6e7eRj?h@hLdqgvnSjVj$e[h]hugxg4c%eCnZj2j(e~hRb)e*e3jygzgAgMd+eaiBgCg,eNdOdTb7c5oDgGgUdHgNn6j9j:efiUn#j'j=egi(jjbVdWdhi?e@e[e9c]eIg^e_e)jjikiYdJgkbZd0ddfefff1dKggfhf2n=j[jjfoipiQgRg!cof%clbmc%n_j|jsfqi1 WbXbqc'c(c)c*c= +c,c5dtfuf6dvfwf-n~jakyfui/nbkekAfxiyiVgYg.cBf^nhkkkDfFiaomkpkFfGihorkukHfHioowkzkJfIivoBkEkLfJiCoGkJkNfKiJoLkOkPfLiQoQkTkRfMi

963  

964cdef CUresult cuGraphMemAllocNodeGetParams(CUgraphNode hNode, CUDA_MEM_ALLOC_NODE_PARAMS* params_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

965 return cydriver._cuGraphMemAllocNodeGetParams(hNode, params_out) 2fKgKhKiKjKkKlKmKnKoKpKqKrKsKtKuKvKwKxKyKzKAKBK{w|w}w~waxbxcxdxexfxgx

966  

967cdef CUresult cuGraphAddMemFreeNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil: 

968 return cydriver._cuGraphAddMemFreeNode(phGraphNode, hGraph, dependencies, numDependencies, dptr) 2~paq;c=c?c9d3 4 5 % Zb0b1bBc%i(i.i:i=i@isrfhdjjjkjqdagpj'h(h+hdbDdEdOePeQeFdfgReSeKjmgWcQj@hVjxg2j3jOdGg9j'jhikikbZd0ddfefff1dKggfhf[jRg%c|jakekYgkkpkukzkEkJkOkTk

969  

970cdef CUresult cuGraphMemFreeNodeGetParams(CUgraphNode hNode, CUdeviceptr* dptr_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

971 return cydriver._cuGraphMemFreeNodeGetParams(hNode, dptr_out) 

972  

973cdef CUresult cuDeviceGraphMemTrim(CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil: 

974 return cydriver._cuDeviceGraphMemTrim(device) 1678

975  

976cdef CUresult cuDeviceGetGraphMemAttribute(CUdevice device, CUgraphMem_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil: 

977 return cydriver._cuDeviceGetGraphMemAttribute(device, attr, value) 26 7 8 fh

978  

979cdef CUresult cuDeviceSetGraphMemAttribute(CUdevice device, CUgraphMem_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil: 

980 return cydriver._cuDeviceSetGraphMemAttribute(device, attr, value) 1678

981  

982cdef CUresult cuGraphClone(CUgraph* phGraphClone, CUgraph originalGraph) except ?CUDA_ERROR_NOT_FOUND nogil: 

983 return cydriver._cuGraphClone(phGraphClone, originalGraph) 2Bb?

984  

985cdef CUresult cuGraphNodeFindInClone(CUgraphNode* phNode, CUgraphNode hOriginalNode, CUgraph hClonedGraph) except ?CUDA_ERROR_NOT_FOUND nogil: 

986 return cydriver._cuGraphNodeFindInClone(phNode, hOriginalNode, hClonedGraph) 

987  

988cdef CUresult cuGraphNodeGetType(CUgraphNode hNode, CUgraphNodeType* typename) except ?CUDA_ERROR_NOT_FOUND nogil: 

989 return cydriver._cuGraphNodeGetType(hNode, typename) 2eKfKgKhKiKjKkKlKmKnKoKpKqKrKsKtKuKvKwKxKyKzKAKBK{w|w}w~waxbxcxCKdxexfxgxd0e0f0g0h0i0j0k0l0m0n0o0p0q0r0s0t0u0v0sbtbubvb2b3b!ob

990  

991cdef CUresult cuGraphNodeGetContainingGraph(CUgraphNode hNode, CUgraph* phGraph) except ?CUDA_ERROR_NOT_FOUND nogil: 

992 return cydriver._cuGraphNodeGetContainingGraph(hNode, phGraph) 

993  

994cdef CUresult cuGraphNodeGetLocalId(CUgraphNode hNode, unsigned int* nodeId) except ?CUDA_ERROR_NOT_FOUND nogil: 

995 return cydriver._cuGraphNodeGetLocalId(hNode, nodeId) 

996  

997cdef CUresult cuGraphNodeGetToolsId(CUgraphNode hNode, unsigned long long* toolsNodeId) except ?CUDA_ERROR_NOT_FOUND nogil: 

998 return cydriver._cuGraphNodeGetToolsId(hNode, toolsNodeId) 

999  

1000cdef CUresult cuGraphGetId(CUgraph hGraph, unsigned int* graphId) except ?CUDA_ERROR_NOT_FOUND nogil: 

1001 return cydriver._cuGraphGetId(hGraph, graphId) 

1002  

1003cdef CUresult cuGraphExecGetId(CUgraphExec hGraphExec, unsigned int* graphId) except ?CUDA_ERROR_NOT_FOUND nogil: 

1004 return cydriver._cuGraphExecGetId(hGraphExec, graphId) 

1005  

1006cdef CUresult cuGraphGetNodes(CUgraph hGraph, CUgraphNode* nodes, size_t* numNodes) except ?CUDA_ERROR_NOT_FOUND nogil: 

1007 return cydriver._cuGraphGetNodes(hGraph, nodes, numNodes) 2Yw9ieKfKgKw0hKiKjKx0kKlKmKnKoKpKy0z0A0B0C0D0E0qKrKF0sKtKuKvKG0H0I0J0wKxKyKzKAKBKK0L0M0N0O0P0Q0R0_w6o7o8o9osbtbubvb2b3b!oM L z A B b Dc

1008  

1009cdef CUresult cuGraphGetRootNodes(CUgraph hGraph, CUgraphNode* rootNodes, size_t* numRootNodes) except ?CUDA_ERROR_NOT_FOUND nogil: 

1010 return cydriver._cuGraphGetRootNodes(hGraph, rootNodes, numRootNodes) 

1011  

1012cdef CUresult cuGraphGetEdges(CUgraph hGraph, CUgraphNode* from_, CUgraphNode* to, CUgraphEdgeData* edgeData, size_t* numEdges) except ?CUDA_ERROR_NOT_FOUND nogil: 

1013 return cydriver._cuGraphGetEdges_v2(hGraph, from_, to, edgeData, numEdges) 2S0T0U0V0W0X0Y09iM L z A B b Dc

1014  

1015cdef CUresult cuGraphNodeGetDependencies(CUgraphNode hNode, CUgraphNode* dependencies, CUgraphEdgeData* edgeData, size_t* numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil: 

1016 return cydriver._cuGraphNodeGetDependencies_v2(hNode, dependencies, edgeData, numDependencies) 2~paq9ieqfqgqQi{w|wZ0}w~waxbx00102030cxCKdxexfxgx405060708090!0#03kT A ?k@kb

1017  

1018cdef CUresult cuGraphNodeGetDependentNodes(CUgraphNode hNode, CUgraphNode* dependentNodes, CUgraphEdgeData* edgeData, size_t* numDependentNodes) except ?CUDA_ERROR_NOT_FOUND nogil: 

1019 return cydriver._cuGraphNodeGetDependentNodes_v2(hNode, dependentNodes, edgeData, numDependentNodes) 29i{w|w}w~waxbxcxCKdxexfxgx$0%0'0(0)0*0z B Ip?k@kb ^k_k

1020  

1021cdef CUresult cuGraphAddDependencies(CUgraph hGraph, const CUgraphNode* from_, const CUgraphNode* to, const CUgraphEdgeData* edgeData, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil: 

1022 return cydriver._cuGraphAddDependencies_v2(hGraph, from_, to, edgeData, numDependencies) 29iz A B Ip?k@kb ^kDc_k

1023  

1024cdef CUresult cuGraphRemoveDependencies(CUgraph hGraph, const CUgraphNode* from_, const CUgraphNode* to, const CUgraphEdgeData* edgeData, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil: 

1025 return cydriver._cuGraphRemoveDependencies_v2(hGraph, from_, to, edgeData, numDependencies) 2B Ip?k@kb

1026  

1027cdef CUresult cuGraphDestroyNode(CUgraphNode hNode) except ?CUDA_ERROR_NOT_FOUND nogil: 

1028 return cydriver._cuGraphDestroyNode(hNode) 2=kL z A DcdK

1029  

1030cdef CUresult cuGraphInstantiate(CUgraphExec* phGraphExec, CUgraph hGraph, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1031 return cydriver._cuGraphInstantiateWithFlags(phGraphExec, hGraph, flags) 2Bb? fh[ `w

1032  

1033cdef CUresult cuGraphInstantiateWithParams(CUgraphExec* phGraphExec, CUgraph hGraph, CUDA_GRAPH_INSTANTIATE_PARAMS* instantiateParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1034 return cydriver._cuGraphInstantiateWithParams(phGraphExec, hGraph, instantiateParams) 2zbAb*fR S 2 W $ nbc d e f g h i j k l m n o p q v r s t u G H I J `c;c=c?c9dX !b{c|cobpbqbYbrb3 4 5 % Zb0b1bBc6W7W8Wbqcqdq!d@c#b$bCbT @ %bM L z A B b 7b8b9b}c~cadw x y D E F O P Q DbEbFb6 7 8 C U V wb4b5b6b

1035  

1036cdef CUresult cuGraphExecGetFlags(CUgraphExec hGraphExec, cuuint64_t* flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1037 return cydriver._cuGraphExecGetFlags(hGraphExec, flags) 

1038  

1039cdef CUresult cuGraphExecKernelNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1040 return cydriver._cuGraphExecKernelNodeSetParams_v2(hGraphExec, hNode, nodeParams) 

1041  

1042cdef CUresult cuGraphExecMemcpyNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_MEMCPY3D* copyParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

1043 return cydriver._cuGraphExecMemcpyNodeSetParams(hGraphExec, hNode, copyParams, ctx) 

1044  

1045cdef CUresult cuGraphExecMemsetNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_MEMSET_NODE_PARAMS* memsetParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

1046 return cydriver._cuGraphExecMemsetNodeSetParams(hGraphExec, hNode, memsetParams, ctx) 

1047  

1048cdef CUresult cuGraphExecHostNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1049 return cydriver._cuGraphExecHostNodeSetParams(hGraphExec, hNode, nodeParams) 

1050  

1051cdef CUresult cuGraphExecChildGraphNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, CUgraph childGraph) except ?CUDA_ERROR_NOT_FOUND nogil: 

1052 return cydriver._cuGraphExecChildGraphNodeSetParams(hGraphExec, hNode, childGraph) 

1053  

1054cdef CUresult cuGraphExecEventRecordNodeSetEvent(CUgraphExec hGraphExec, CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil: 

1055 return cydriver._cuGraphExecEventRecordNodeSetEvent(hGraphExec, hNode, event) 

1056  

1057cdef CUresult cuGraphExecEventWaitNodeSetEvent(CUgraphExec hGraphExec, CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil: 

1058 return cydriver._cuGraphExecEventWaitNodeSetEvent(hGraphExec, hNode, event) 

1059  

1060cdef CUresult cuGraphExecExternalSemaphoresSignalNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1061 return cydriver._cuGraphExecExternalSemaphoresSignalNodeSetParams(hGraphExec, hNode, nodeParams) 

1062  

1063cdef CUresult cuGraphExecExternalSemaphoresWaitNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_EXT_SEM_WAIT_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1064 return cydriver._cuGraphExecExternalSemaphoresWaitNodeSetParams(hGraphExec, hNode, nodeParams) 

1065  

1066cdef CUresult cuGraphNodeSetEnabled(CUgraphExec hGraphExec, CUgraphNode hNode, unsigned int isEnabled) except ?CUDA_ERROR_NOT_FOUND nogil: 

1067 return cydriver._cuGraphNodeSetEnabled(hGraphExec, hNode, isEnabled) 

1068  

1069cdef CUresult cuGraphNodeGetEnabled(CUgraphExec hGraphExec, CUgraphNode hNode, unsigned int* isEnabled) except ?CUDA_ERROR_NOT_FOUND nogil: 

1070 return cydriver._cuGraphNodeGetEnabled(hGraphExec, hNode, isEnabled) 

1071  

1072cdef CUresult cuGraphUpload(CUgraphExec hGraphExec, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1073 return cydriver._cuGraphUpload(hGraphExec, hStream) 2S $ `c;c=c?cX !b{c|cobpbqbrb3 4 5 Zb0b1b#b$b%bw x y D E F O P Q DbEbFb6 7 8

1074  

1075cdef CUresult cuGraphLaunch(CUgraphExec hGraphExec, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1076 return cydriver._cuGraphLaunch(hGraphExec, hStream) 2zbAbR S W $ c d e f g h i j k l m n o p q v r s t u G H I J `c;c=c?c9dX !b{c|cobpbqbYbrb3 4 5 % Zb0b1bBc@c#b$bBbCbT ? @ %bM L z A B b w x y D E F O P Q DbEbFb6 7 8 C U V fh[

1077  

1078cdef CUresult cuGraphExecDestroy(CUgraphExec hGraphExec) except ?CUDA_ERROR_NOT_FOUND nogil: 

1079 return cydriver._cuGraphExecDestroy(hGraphExec) 2zbAb*fR S 2 W $ nbc d e f g h i j k l m n o p q v r s t u G H I J `c;c=c?c9dX !b{c|cobpbqbYbrb3 4 5 % Zb0b1bBc6W7W8Wbqcqdq!d@c#b$bCbT @ %bM L z A B b 7b8b9b}c~cadw x y D E F O P Q DbEbFb6 7 8 C U V wb4b5b6b[ `w

1080  

1081cdef CUresult cuGraphDestroy(CUgraph hGraph) except ?CUDA_ERROR_NOT_FOUND nogil: 

1082 return cydriver._cuGraphDestroy(hGraph) 2zbAb*fR S 4i2 W $ nbc d e f g h i j k l m n o p q v r s t u G H I J fBgBhBiBjBkBlBmBnBoBpBqBrBsBtBuBvBwBxByBzB9iABBBCBDBX EB,tFBGBHBIBJBKBLBMBNBOBPBQBRBSBTBUBVBWBXBYBZB0B1B2B3B4B5B6B(b7B-t.t8B9B!B#B$B%B'B(B)B*B+B,B-B.B)b/B/t:t:B;B=B?B@B[B]B^B_B`B{B|B}B~BaCbCcCdCeCfCgChCiC*bjCkC;t=tlCmCnCoCpCqCrCsCtCuCvCwCxCyCzC+bACBC?t@tCCDCECFCGCHCICJCKCLCMCNCOCPCQC,bRCSC[t]tTCUCVCWCXCYCZC0C1C2C3C4C5C6C7C-b8C9C^t_t!C#C$C%C'C(C)C*C+C,C-C.C/C:C;C=C?C@C[C]C^C_C`C{C|C=k}C~CaDbDcDdD[k0W1W2W3WZw4W_wsr3khq!d]k@c6o7o8o9osbtbubvb#b$b2bch#d5iBbCb$d6i(fT ? @ 3b%bM L z A B bKIp?k@kb ^kDc_k7b8b9b}c~cadw x y D E F O P Q DbEbFb6 7 8 C U V wb4b5b[c6bN fh[ 5WYheD?bgDhDiD`t{tkDlDmDnDoDpDqDrDsDuDvDyD@bADBDCD|t}tEDFDGDHDIDJDKDLDMDODPDJbQD~tauRDSDTDUDVDWDXDYDZDbu9 cudueuBqCqfuguhuiujukulumunuoupu~ quabruMb3D) 4D* 5D+ 6D, 7D8Dbb9D!Dsutu#D$D%D'D(D)D*D+D,D-D.D[b:D;D=Duuvu?D@D[D]D^D_D`D{D|D}D~DaENbcEdEeEwuxugEhEiEjEkElEmEnEoEqErEsEcbtEyuzuuEvEwExEyEzEAEBECEAuObCuDuEuFuGuHuIuJuKuLuMuNuOuPuQuRuSuTuUuVuWuXuYuZu0u1u2udbHE3u4uIEJEKELEMENEOEPE]bQERESE5u6uTEUEVEWEXEYEZE0E1E2E3E4E5E6E7E8E9E!E#E$E^b%E'E(E7u8u)E*E+E,E-E.E/E:E;E=E?E_b@E9u!u[E]E^E_E`E{E|E}E~EacaFbFcF#u$udFeFfFgFhFiFjFkFlFmFnF0 oF%u'upFqFrFsFtF- uF(u)uvFwFxFyFzFAFBFccCFDFEF*u+uFFGFHFIFJFKFLFMFNFOFPFQFdcRFSF,u-uTFUFVFWFXFYFZF0F1F.ufb:u;u=uDqEq@u[u]u^u_u`u{u|u}u~uav6F7Fec9F!F#Fbvcv%F'F(F)F*F+F,F-F.F:F;FRb=Fdvev?F@F[F]F^F_F`F{F|Ffv! gvhvivFqGqjvkvlvmvnvovpvqvrvsvtvgbuvhbvvUbbG. cG/ dG: eG; fGgGibhGiGwvxvjGkGlGmGnGoGpGqGrGsGtGfcvGwGxGyvzvyGzGAGBGCGDGEGFGGGHGIGJGgcLGMGNGAvBvPGQGRGSGTGUGVGWGXGZG0G1Gjb2GCvDv3G4G5G6G7G8G9G!G#GEvVbGvHvIvJvKvLvMvNvOvPvQvRvSvTvUvVvWvXvYvZv0v1v2v3v4v5v6vkb)G7v8v*G+G,G-G.G/G:G;Ghc=G?G@G9v!v[G]G^G_G`G{G|G}G~GaHbHcHdHeHfHgHhHiHjHkHiclHmHnH#v$voHpHqHrHsHtHuHvHwHxHyHjczH%v'vAHBHCHDHEHFHGHHHIHpcJHKHLH(v)vMHNHOHPHQHRHSHTHUHVHWH1 XH*v+vYHZH0H1H2H= 3H,v-v4H5H6H7H8H9H!Hrc#H$H%H.v/v'H(H)H*H+H,H-H.H/H:H;H=Hsc?H@H:v;v[H]H^H_H`H{H|H}H~H=vmb@v[v]vHqIq_v`v{v|v}v~vawbwcwdweweIfItchIiIjIfwgwlImInIoIpIqIrIsItIvIwIxIuczIAIBIhwiwDIEIFIGIHIIIJIKILINIOIPIvcRISITIjwkwVIWIXIYIZI0I1I2I3I5I6I7Iwc9I!I#Ilwmw%I'I(I)I*I+I,I-I.I:I;I=Ixc@I[I]Inwow_I`I{I|I}I~IaJbJcJeJfJgJyciJjJkJpwqwmJnJoJpJqJrJsJtJuJwJxJyJzcAJBJCJrwswEJFJGJHJIJJJKJLJMJOJPJQJAcSJTJUJtwuwWJXJYJZJ0J1J2J3J4J6J7J

1083  

1084cdef CUresult cuGraphExecUpdate(CUgraphExec hGraphExec, CUgraph hGraph, CUgraphExecUpdateResultInfo* resultInfo) except ?CUDA_ERROR_NOT_FOUND nogil: 

1085 return cydriver._cuGraphExecUpdate_v2(hGraphExec, hGraph, resultInfo) 2C U V wb

1086  

1087cdef CUresult cuGraphKernelNodeCopyAttributes(CUgraphNode dst, CUgraphNode src) except ?CUDA_ERROR_NOT_FOUND nogil: 

1088 return cydriver._cuGraphKernelNodeCopyAttributes(dst, src) 

1089  

1090cdef CUresult cuGraphKernelNodeGetAttribute(CUgraphNode hNode, CUkernelNodeAttrID attr, CUkernelNodeAttrValue* value_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

1091 return cydriver._cuGraphKernelNodeGetAttribute(hNode, attr, value_out) 

1092  

1093cdef CUresult cuGraphKernelNodeSetAttribute(CUgraphNode hNode, CUkernelNodeAttrID attr, const CUkernelNodeAttrValue* value) except ?CUDA_ERROR_NOT_FOUND nogil: 

1094 return cydriver._cuGraphKernelNodeSetAttribute(hNode, attr, value) 

1095  

1096cdef CUresult cuGraphDebugDotPrint(CUgraph hGraph, const char* path, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1097 return cydriver._cuGraphDebugDotPrint(hGraph, path, flags) 2XtYtN

1098  

1099cdef CUresult cuUserObjectCreate(CUuserObject* object_out, void* ptr, CUhostFn destroy, unsigned int initialRefcount, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1100 return cydriver._cuUserObjectCreate(object_out, ptr, destroy, initialRefcount, flags) 2zbAb`cX !b{c|cobpbqbYbrbQi2k(b*d+dblclbd)b-d.djlklcd*b:d;dzlAldd+b?d@dHlIled,b]d^dOlPlfd-b`d{dWlXlgd!dsbtbubvb#b$b2bch#d5iBbCb$d6i(fT ? @ 3b%bM L z A B b V ?bbjcjLqoe@bhjij)mqeJbsete[fod9 OcPcrdKb~ abMb) * + , bb}f~f8hRc[bnjoj@myeNb$h%hrjxdcbzdAdAeScObzjAjBjBd,h-hGeHeIeJe.hKeLeMeNedbDdEdOe]bIjJjbnTegghgigjg^bGdHdVeYe_bUcVcWcId`b{beb|b}b~bacOjPjmn2e0 PbQbbc- 1c2cJdcc8e9eng!edcTjUjwn#efbvgwg^h3cec0j1jDn'eRb)e*eygMd! 5c6cPdSbgbhbUb. / : ; ibEgFgei8cfc7j8jOn/egc$j%jVn;ejbVdWd?e9cVb*j+j,jXdlimi`e{e|e}eni~eafbfcfkbZd0ddfhc?j@j3nifLgMgNgOgic2d3dkfnfjc#c$c%c4dkclclbmcncocpc`j{j'nrf1 WbXbqc= +c,c5drcSgTgrixfscckdk:nzfmbWgXgzi-ctcikjk_nCfucnkokboEfvcsktkioGfwcxkykpoIfxcCkDkwoKfycHkIkDoMfzcMkNkKoOfAcRkSkRoQf

1101  

1102cdef CUresult cuUserObjectRetain(CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil: 

1103 return cydriver._cuUserObjectRetain(object, count) 

1104  

1105cdef CUresult cuUserObjectRelease(CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil: 

1106 return cydriver._cuUserObjectRelease(object, count) 

1107  

1108cdef CUresult cuGraphRetainUserObject(CUgraph graph, CUuserObject object, unsigned int count, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1109 return cydriver._cuGraphRetainUserObject(graph, object, count, flags) 2zbAb`cX !b{c|cobpbqbYbrbQi2k(b*d+dblclbd)b-d.djlklcd*b:d;dzlAldd+b?d@dHlIled,b]d^dOlPlfd-b`d{dWlXlgd!dsbtbubvb#b$b2bch#d5iBbCb$d6i(fT ? @ 3b%bM L z A B b V ?bbjcjLqoe@bhjij)mqeJbsete[fod9 OcPcrdKb~ abMb) * + , bb}f~f8hRc[bnjoj@myeNb$h%hrjxdcbzdAdAeScObzjAjBjBd,h-hGeHeIeJe.hKeLeMeNedbDdEdOe]bIjJjbnTegghgigjg^bGdHdVeYe_bUcVcWcId`b{beb|b}b~bacOjPjmn2e0 PbQbbc- 1c2cJdcc8e9eng!edcTjUjwn#efbvgwg^h3cec0j1jDn'eRb)e*eygMd! 5c6cPdSbgbhbUb. / : ; ibEgFgei8cfc7j8jOn/egc$j%jVn;ejbVdWd?e9cVb*j+j,jXdlimi`e{e|e}eni~eafbfcfkbZd0ddfhc?j@j3nifLgMgNgOgic2d3dkfnfjc#c$c%c4dkclclbmcncocpc`j{j'nrf1 WbXbqc= +c,c5drcSgTgrixfscckdk:nzfmbWgXgzi-ctcikjk_nCfucnkokboEfvcsktkioGfwcxkykpoIfxcCkDkwoKfycHkIkDoMfzcMkNkKoOfAcRkSkRoQf

1110  

1111cdef CUresult cuGraphReleaseUserObject(CUgraph graph, CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil: 

1112 return cydriver._cuGraphReleaseUserObject(graph, object, count) 

1113  

1114cdef CUresult cuGraphAddNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1115 return cydriver._cuGraphAddNode_v2(phGraphNode, hGraph, dependencies, dependencyData, numDependencies, nodeParams) 2c d e f g h i j k l m n o p q v r s t u G H I J YwdlelflglllmlnlolBlClDlElJlKlJqLlQlRlSlTlYlZl0l1l[k]k6o7o8o9osbtbubvb!oC N cK[ 9m!m$m%m*m+m-m.m]f^f_f`fsdtdudvd) * + , /m:m;m=m[m]m_m`msjtjvjwjBeCeEeFeCjDjFjGjGeHeIeJeKeLeMeNePeQeReSecndnenfngghgigjggnhninjnknWeXe0e1e`b{b}b~bnnonqnrnXcYcZc0c4e5e6e7eogpgrgsgxnynznAn_h`h|h}hBnEnFnHnInzgAgBgCgQdRdSdTd. / : ; JnKnLnMnPnQnSnTnWnXnZn0n@e[e^e_e-j.j:j;j`e{e|e}e~eafbfcfefffgfhf4n5n6n7nLgMgNgOg8n9n!n#n$nlfmfpfqfkclcncoc(n)n+n,n'c(c)c*ctfufvfwfsitiviwi;n=n?n@nAiBiDiEi]n`n{n}n~ncodofogojokomonoqorotouoxoyoAoBoEoFoHoIoLoMoOoPoSoToVoWo

1116  

1117cdef CUresult cuGraphNodeSetParams(CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1118 return cydriver._cuGraphNodeSetParams(hNode, nodeParams) 1[

1119  

1120cdef CUresult cuGraphNodeGetParams(CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1121 return cydriver._cuGraphNodeGetParams(hNode, nodeParams) 

1122  

1123cdef CUresult cuGraphExecNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1124 return cydriver._cuGraphExecNodeSetParams(hGraphExec, hNode, nodeParams) 1[

1125  

1126cdef CUresult cuGraphConditionalHandleCreate(CUgraphConditionalHandle* pHandle_out, CUgraph hGraph, CUcontext ctx, unsigned int defaultLaunchValue, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1127 return cydriver._cuGraphConditionalHandleCreate(pHandle_out, hGraph, ctx, defaultLaunchValue, flags) 2c d e f g h i j k l m n o p q v r s t u G H I J YwdlelflglllmlnlolBlClDlElJlKlJqLlQlRlSlTlYlZl0l1l[kZw]k6o7o8o9osbtbubvb!oC N cKTp9m!m$m%mVp*m+m-m.m]f^f_f`fwesdtdudvd) * + , 7hbb|f}f~fag8h/m:mRcwdbgXp;m=mYp[m]m_m`m{msjtjvjwjBeCeEeFe}mCjDjFjGjGeHeIeJeKeLeMeNePeQeReSe1pcndnenfngghgigjggnhninjnknkgWeXe0e1e`b{b}b~bWwnnonqnrnXcYcZc0c4e5e6e7e=hogpgrgsgxnynznAnWj_h`h|h}hBn6pEnFnHnInzgAgBgCg-eQdRdSdTd. / : ; 5oibDgEgFgGgeiJnKn8cUdHg8pLnMn9pPnQnSnTn!pWnXnZn0n@e[e^e_e1n-j.j:j;j`e{e|e}e~eafbfcfefffgfhf$p4n5n6n7nLgMgNgOg8n9n!n#n$nPglfmfpfqfkclcncoc%p(n)n+n,n'c(c)c*ctfufvfwf}jsitiviwi;n=n?n@nfkAiBiDiEi]n+p`n{n}n~n/pcodofogo;pjokomono?pqorotouo[pxoyoAoBo^pEoFoHoIo`pLoMoOoPo{pSoToVoWo

1128  

1129cdef CUresult cuOccupancyMaxActiveBlocksPerMultiprocessor(int* numBlocks, CUfunction func, int blockSize, size_t dynamicSMemSize) except ?CUDA_ERROR_NOT_FOUND nogil: 

1130 return cydriver._cuOccupancyMaxActiveBlocksPerMultiprocessor(numBlocks, func, blockSize, dynamicSMemSize) 2(d1t2t3t4t5t6t7t8t9t!t#t$t%t't(t)t*t+t

1131  

1132cdef CUresult cuOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(int* numBlocks, CUfunction func, int blockSize, size_t dynamicSMemSize, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1133 return cydriver._cuOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(numBlocks, func, blockSize, dynamicSMemSize, flags) 

1134  

1135cdef CUresult cuOccupancyMaxPotentialBlockSize(int* minGridSize, int* blockSize, CUfunction func, CUoccupancyB2DSize blockSizeToDynamicSMemSize, size_t dynamicSMemSize, int blockSizeLimit) except ?CUDA_ERROR_NOT_FOUND nogil: 

1136 return cydriver._cuOccupancyMaxPotentialBlockSize(minGridSize, blockSize, func, blockSizeToDynamicSMemSize, dynamicSMemSize, blockSizeLimit) 2.A/A:A;A=A?A@A[A]A^A_A`A{A|A}A~AaBbBcBdBeB

1137  

1138cdef CUresult cuOccupancyMaxPotentialBlockSizeWithFlags(int* minGridSize, int* blockSize, CUfunction func, CUoccupancyB2DSize blockSizeToDynamicSMemSize, size_t dynamicSMemSize, int blockSizeLimit, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1139 return cydriver._cuOccupancyMaxPotentialBlockSizeWithFlags(minGridSize, blockSize, func, blockSizeToDynamicSMemSize, dynamicSMemSize, blockSizeLimit, flags) 

1140  

1141cdef CUresult cuOccupancyAvailableDynamicSMemPerBlock(size_t* dynamicSmemSize, CUfunction func, int numBlocks, int blockSize) except ?CUDA_ERROR_NOT_FOUND nogil: 

1142 return cydriver._cuOccupancyAvailableDynamicSMemPerBlock(dynamicSmemSize, func, numBlocks, blockSize) 2(A)A*A+A,A-A

1143  

1144cdef CUresult cuOccupancyMaxPotentialClusterSize(int* clusterSize, CUfunction func, const CUlaunchConfig* config) except ?CUDA_ERROR_NOT_FOUND nogil: 

1145 return cydriver._cuOccupancyMaxPotentialClusterSize(clusterSize, func, config) 

1146  

1147cdef CUresult cuOccupancyMaxActiveClusters(int* numClusters, CUfunction func, const CUlaunchConfig* config) except ?CUDA_ERROR_NOT_FOUND nogil: 

1148 return cydriver._cuOccupancyMaxActiveClusters(numClusters, func, config) 

1149  

1150cdef CUresult cuTexRefSetArray(CUtexref hTexRef, CUarray hArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1151 return cydriver._cuTexRefSetArray(hTexRef, hArray, Flags) 

1152  

1153cdef CUresult cuTexRefSetMipmappedArray(CUtexref hTexRef, CUmipmappedArray hMipmappedArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1154 return cydriver._cuTexRefSetMipmappedArray(hTexRef, hMipmappedArray, Flags) 

1155  

1156cdef CUresult cuTexRefSetAddress(size_t* ByteOffset, CUtexref hTexRef, CUdeviceptr dptr, size_t numbytes) except ?CUDA_ERROR_NOT_FOUND nogil: 

1157 return cydriver._cuTexRefSetAddress_v2(ByteOffset, hTexRef, dptr, numbytes) 

1158  

1159cdef CUresult cuTexRefSetAddress2D(CUtexref hTexRef, const CUDA_ARRAY_DESCRIPTOR* desc, CUdeviceptr dptr, size_t Pitch) except ?CUDA_ERROR_NOT_FOUND nogil: 

1160 return cydriver._cuTexRefSetAddress2D_v3(hTexRef, desc, dptr, Pitch) 

1161  

1162cdef CUresult cuTexRefSetFormat(CUtexref hTexRef, CUarray_format fmt, int NumPackedComponents) except ?CUDA_ERROR_NOT_FOUND nogil: 

1163 return cydriver._cuTexRefSetFormat(hTexRef, fmt, NumPackedComponents) 

1164  

1165cdef CUresult cuTexRefSetAddressMode(CUtexref hTexRef, int dim, CUaddress_mode am) except ?CUDA_ERROR_NOT_FOUND nogil: 

1166 return cydriver._cuTexRefSetAddressMode(hTexRef, dim, am) 

1167  

1168cdef CUresult cuTexRefSetFilterMode(CUtexref hTexRef, CUfilter_mode fm) except ?CUDA_ERROR_NOT_FOUND nogil: 

1169 return cydriver._cuTexRefSetFilterMode(hTexRef, fm) 

1170  

1171cdef CUresult cuTexRefSetMipmapFilterMode(CUtexref hTexRef, CUfilter_mode fm) except ?CUDA_ERROR_NOT_FOUND nogil: 

1172 return cydriver._cuTexRefSetMipmapFilterMode(hTexRef, fm) 

1173  

1174cdef CUresult cuTexRefSetMipmapLevelBias(CUtexref hTexRef, float bias) except ?CUDA_ERROR_NOT_FOUND nogil: 

1175 return cydriver._cuTexRefSetMipmapLevelBias(hTexRef, bias) 

1176  

1177cdef CUresult cuTexRefSetMipmapLevelClamp(CUtexref hTexRef, float minMipmapLevelClamp, float maxMipmapLevelClamp) except ?CUDA_ERROR_NOT_FOUND nogil: 

1178 return cydriver._cuTexRefSetMipmapLevelClamp(hTexRef, minMipmapLevelClamp, maxMipmapLevelClamp) 

1179  

1180cdef CUresult cuTexRefSetMaxAnisotropy(CUtexref hTexRef, unsigned int maxAniso) except ?CUDA_ERROR_NOT_FOUND nogil: 

1181 return cydriver._cuTexRefSetMaxAnisotropy(hTexRef, maxAniso) 

1182  

1183cdef CUresult cuTexRefSetBorderColor(CUtexref hTexRef, float* pBorderColor) except ?CUDA_ERROR_NOT_FOUND nogil: 

1184 return cydriver._cuTexRefSetBorderColor(hTexRef, pBorderColor) 

1185  

1186cdef CUresult cuTexRefSetFlags(CUtexref hTexRef, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1187 return cydriver._cuTexRefSetFlags(hTexRef, Flags) 

1188  

1189cdef CUresult cuTexRefGetAddress(CUdeviceptr* pdptr, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1190 return cydriver._cuTexRefGetAddress_v2(pdptr, hTexRef) 

1191  

1192cdef CUresult cuTexRefGetArray(CUarray* phArray, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1193 return cydriver._cuTexRefGetArray(phArray, hTexRef) 

1194  

1195cdef CUresult cuTexRefGetMipmappedArray(CUmipmappedArray* phMipmappedArray, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1196 return cydriver._cuTexRefGetMipmappedArray(phMipmappedArray, hTexRef) 

1197  

1198cdef CUresult cuTexRefGetAddressMode(CUaddress_mode* pam, CUtexref hTexRef, int dim) except ?CUDA_ERROR_NOT_FOUND nogil: 

1199 return cydriver._cuTexRefGetAddressMode(pam, hTexRef, dim) 

1200  

1201cdef CUresult cuTexRefGetFilterMode(CUfilter_mode* pfm, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1202 return cydriver._cuTexRefGetFilterMode(pfm, hTexRef) 

1203  

1204cdef CUresult cuTexRefGetFormat(CUarray_format* pFormat, int* pNumChannels, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1205 return cydriver._cuTexRefGetFormat(pFormat, pNumChannels, hTexRef) 

1206  

1207cdef CUresult cuTexRefGetMipmapFilterMode(CUfilter_mode* pfm, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1208 return cydriver._cuTexRefGetMipmapFilterMode(pfm, hTexRef) 

1209  

1210cdef CUresult cuTexRefGetMipmapLevelBias(float* pbias, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1211 return cydriver._cuTexRefGetMipmapLevelBias(pbias, hTexRef) 

1212  

1213cdef CUresult cuTexRefGetMipmapLevelClamp(float* pminMipmapLevelClamp, float* pmaxMipmapLevelClamp, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1214 return cydriver._cuTexRefGetMipmapLevelClamp(pminMipmapLevelClamp, pmaxMipmapLevelClamp, hTexRef) 

1215  

1216cdef CUresult cuTexRefGetMaxAnisotropy(int* pmaxAniso, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1217 return cydriver._cuTexRefGetMaxAnisotropy(pmaxAniso, hTexRef) 

1218  

1219cdef CUresult cuTexRefGetBorderColor(float* pBorderColor, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1220 return cydriver._cuTexRefGetBorderColor(pBorderColor, hTexRef) 

1221  

1222cdef CUresult cuTexRefGetFlags(unsigned int* pFlags, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1223 return cydriver._cuTexRefGetFlags(pFlags, hTexRef) 

1224  

1225cdef CUresult cuTexRefCreate(CUtexref* pTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1226 return cydriver._cuTexRefCreate(pTexRef) 

1227  

1228cdef CUresult cuTexRefDestroy(CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1229 return cydriver._cuTexRefDestroy(hTexRef) 

1230  

1231cdef CUresult cuSurfRefSetArray(CUsurfref hSurfRef, CUarray hArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1232 return cydriver._cuSurfRefSetArray(hSurfRef, hArray, Flags) 

1233  

1234cdef CUresult cuSurfRefGetArray(CUarray* phArray, CUsurfref hSurfRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1235 return cydriver._cuSurfRefGetArray(phArray, hSurfRef) 

1236  

1237cdef CUresult cuTexObjectCreate(CUtexObject* pTexObject, const CUDA_RESOURCE_DESC* pResDesc, const CUDA_TEXTURE_DESC* pTexDesc, const CUDA_RESOURCE_VIEW_DESC* pResViewDesc) except ?CUDA_ERROR_NOT_FOUND nogil: 

1238 return cydriver._cuTexObjectCreate(pTexObject, pResDesc, pTexDesc, pResViewDesc) 

1239  

1240cdef CUresult cuTexObjectDestroy(CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil: 

1241 return cydriver._cuTexObjectDestroy(texObject) 

1242  

1243cdef CUresult cuTexObjectGetResourceDesc(CUDA_RESOURCE_DESC* pResDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil: 

1244 return cydriver._cuTexObjectGetResourceDesc(pResDesc, texObject) 

1245  

1246cdef CUresult cuTexObjectGetTextureDesc(CUDA_TEXTURE_DESC* pTexDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil: 

1247 return cydriver._cuTexObjectGetTextureDesc(pTexDesc, texObject) 

1248  

1249cdef CUresult cuTexObjectGetResourceViewDesc(CUDA_RESOURCE_VIEW_DESC* pResViewDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil: 

1250 return cydriver._cuTexObjectGetResourceViewDesc(pResViewDesc, texObject) 

1251  

1252cdef CUresult cuSurfObjectCreate(CUsurfObject* pSurfObject, const CUDA_RESOURCE_DESC* pResDesc) except ?CUDA_ERROR_NOT_FOUND nogil: 

1253 return cydriver._cuSurfObjectCreate(pSurfObject, pResDesc) 

1254  

1255cdef CUresult cuSurfObjectDestroy(CUsurfObject surfObject) except ?CUDA_ERROR_NOT_FOUND nogil: 

1256 return cydriver._cuSurfObjectDestroy(surfObject) 

1257  

1258cdef CUresult cuSurfObjectGetResourceDesc(CUDA_RESOURCE_DESC* pResDesc, CUsurfObject surfObject) except ?CUDA_ERROR_NOT_FOUND nogil: 

1259 return cydriver._cuSurfObjectGetResourceDesc(pResDesc, surfObject) 

1260  

1261cdef CUresult cuTensorMapEncodeTiled(CUtensorMap* tensorMap, CUtensorMapDataType tensorDataType, cuuint32_t tensorRank, void* globalAddress, const cuuint64_t* globalDim, const cuuint64_t* globalStrides, const cuuint32_t* boxDim, const cuuint32_t* elementStrides, CUtensorMapInterleave interleave, CUtensorMapSwizzle swizzle, CUtensorMapL2promotion l2Promotion, CUtensorMapFloatOOBfill oobFill) except ?CUDA_ERROR_NOT_FOUND nogil: 

1262 return cydriver._cuTensorMapEncodeTiled(tensorMap, tensorDataType, tensorRank, globalAddress, globalDim, globalStrides, boxDim, elementStrides, interleave, swizzle, l2Promotion, oobFill) 

1263  

1264cdef CUresult cuTensorMapEncodeIm2col(CUtensorMap* tensorMap, CUtensorMapDataType tensorDataType, cuuint32_t tensorRank, void* globalAddress, const cuuint64_t* globalDim, const cuuint64_t* globalStrides, const int* pixelBoxLowerCorner, const int* pixelBoxUpperCorner, cuuint32_t channelsPerPixel, cuuint32_t pixelsPerColumn, const cuuint32_t* elementStrides, CUtensorMapInterleave interleave, CUtensorMapSwizzle swizzle, CUtensorMapL2promotion l2Promotion, CUtensorMapFloatOOBfill oobFill) except ?CUDA_ERROR_NOT_FOUND nogil: 

1265 return cydriver._cuTensorMapEncodeIm2col(tensorMap, tensorDataType, tensorRank, globalAddress, globalDim, globalStrides, pixelBoxLowerCorner, pixelBoxUpperCorner, channelsPerPixel, pixelsPerColumn, elementStrides, interleave, swizzle, l2Promotion, oobFill) 

1266  

1267cdef CUresult cuTensorMapEncodeIm2colWide(CUtensorMap* tensorMap, CUtensorMapDataType tensorDataType, cuuint32_t tensorRank, void* globalAddress, const cuuint64_t* globalDim, const cuuint64_t* globalStrides, int pixelBoxLowerCornerWidth, int pixelBoxUpperCornerWidth, cuuint32_t channelsPerPixel, cuuint32_t pixelsPerColumn, const cuuint32_t* elementStrides, CUtensorMapInterleave interleave, CUtensorMapIm2ColWideMode mode, CUtensorMapSwizzle swizzle, CUtensorMapL2promotion l2Promotion, CUtensorMapFloatOOBfill oobFill) except ?CUDA_ERROR_NOT_FOUND nogil: 

1268 return cydriver._cuTensorMapEncodeIm2colWide(tensorMap, tensorDataType, tensorRank, globalAddress, globalDim, globalStrides, pixelBoxLowerCornerWidth, pixelBoxUpperCornerWidth, channelsPerPixel, pixelsPerColumn, elementStrides, interleave, mode, swizzle, l2Promotion, oobFill) 

1269  

1270cdef CUresult cuTensorMapReplaceAddress(CUtensorMap* tensorMap, void* globalAddress) except ?CUDA_ERROR_NOT_FOUND nogil: 

1271 return cydriver._cuTensorMapReplaceAddress(tensorMap, globalAddress) 

1272  

1273cdef CUresult cuDeviceCanAccessPeer(int* canAccessPeer, CUdevice dev, CUdevice peerDev) except ?CUDA_ERROR_NOT_FOUND nogil: 

1274 return cydriver._cuDeviceCanAccessPeer(canAccessPeer, dev, peerDev) 

1275  

1276cdef CUresult cuCtxEnablePeerAccess(CUcontext peerContext, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1277 return cydriver._cuCtxEnablePeerAccess(peerContext, Flags) 

1278  

1279cdef CUresult cuCtxDisablePeerAccess(CUcontext peerContext) except ?CUDA_ERROR_NOT_FOUND nogil: 

1280 return cydriver._cuCtxDisablePeerAccess(peerContext) 

1281  

1282cdef CUresult cuDeviceGetP2PAttribute(int* value, CUdevice_P2PAttribute attrib, CUdevice srcDevice, CUdevice dstDevice) except ?CUDA_ERROR_NOT_FOUND nogil: 

1283 return cydriver._cuDeviceGetP2PAttribute(value, attrib, srcDevice, dstDevice) 

1284  

1285cdef CUresult cuDeviceGetP2PAtomicCapabilities(unsigned int* capabilities, const CUatomicOperation* operations, unsigned int count, CUdevice srcDevice, CUdevice dstDevice) except ?CUDA_ERROR_NOT_FOUND nogil: 

1286 return cydriver._cuDeviceGetP2PAtomicCapabilities(capabilities, operations, count, srcDevice, dstDevice) 

1287  

1288cdef CUresult cuGraphicsUnregisterResource(CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil: 

1289 return cydriver._cuGraphicsUnregisterResource(resource) 2=k4g5g6g3o9W!W#W$W%W'W7g8g9g1i!gqr#g(W$gGh)W*W+W

1290  

1291cdef CUresult cuGraphicsSubResourceGetMappedArray(CUarray* pArray, CUgraphicsResource resource, unsigned int arrayIndex, unsigned int mipLevel) except ?CUDA_ERROR_NOT_FOUND nogil: 

1292 return cydriver._cuGraphicsSubResourceGetMappedArray(pArray, resource, arrayIndex, mipLevel) 

1293  

1294cdef CUresult cuGraphicsResourceGetMappedMipmappedArray(CUmipmappedArray* pMipmappedArray, CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil: 

1295 return cydriver._cuGraphicsResourceGetMappedMipmappedArray(pMipmappedArray, resource) 

1296  

1297cdef CUresult cuGraphicsResourceGetMappedPointer(CUdeviceptr* pDevPtr, size_t* pSize, CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil: 

1298 return cydriver._cuGraphicsResourceGetMappedPointer_v2(pDevPtr, pSize, resource) 24g2o5g6g7g8g9g1i!gqr#g$g9k

1299  

1300cdef CUresult cuGraphicsResourceSetMapFlags(CUgraphicsResource resource, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1301 return cydriver._cuGraphicsResourceSetMapFlags_v2(resource, flags) 

1302  

1303cdef CUresult cuGraphicsMapResources(unsigned int count, CUgraphicsResource* resources, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1304 return cydriver._cuGraphicsMapResources(count, resources, hStream) 24g2o5g6g7g8g9g1i!gqr#g$g9k

1305  

1306cdef CUresult cuGraphicsUnmapResources(unsigned int count, CUgraphicsResource* resources, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1307 return cydriver._cuGraphicsUnmapResources(count, resources, hStream) 2=k4g5g6g7g8g9g1i!gqr#g$g9k

1308  

1309cdef CUresult cuGetProcAddress(const char* symbol, void** pfn, int cudaVersion, cuuint64_t flags, CUdriverProcAddressQueryResult* symbolStatus) except ?CUDA_ERROR_NOT_FOUND nogil: 

1310 return cydriver._cuGetProcAddress_v2(symbol, pfn, cudaVersion, flags, symbolStatus) 

1311  

1312cdef CUresult cuCoredumpGetAttribute(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil: 

1313 return cydriver._cuCoredumpGetAttribute(attrib, value, size) 

1314  

1315cdef CUresult cuCoredumpGetAttributeGlobal(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil: 

1316 return cydriver._cuCoredumpGetAttributeGlobal(attrib, value, size) 2,W

1317  

1318cdef CUresult cuCoredumpSetAttribute(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil: 

1319 return cydriver._cuCoredumpSetAttribute(attrib, value, size) 

1320  

1321cdef CUresult cuCoredumpSetAttributeGlobal(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil: 

1322 return cydriver._cuCoredumpSetAttributeGlobal(attrib, value, size) 2,W

1323  

1324cdef CUresult cuCoredumpRegisterStartCallback(CUcoredumpStatusCallback callback, void* userData, CUcoredumpCallbackHandle* callbackOut) except ?CUDA_ERROR_NOT_FOUND nogil: 

1325 return cydriver._cuCoredumpRegisterStartCallback(callback, userData, callbackOut) 

1326  

1327cdef CUresult cuCoredumpRegisterCompleteCallback(CUcoredumpStatusCallback callback, void* userData, CUcoredumpCallbackHandle* callbackOut) except ?CUDA_ERROR_NOT_FOUND nogil: 

1328 return cydriver._cuCoredumpRegisterCompleteCallback(callback, userData, callbackOut) 

1329  

1330cdef CUresult cuCoredumpDeregisterStartCallback(CUcoredumpCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil: 

1331 return cydriver._cuCoredumpDeregisterStartCallback(callback) 

1332  

1333cdef CUresult cuCoredumpDeregisterCompleteCallback(CUcoredumpCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil: 

1334 return cydriver._cuCoredumpDeregisterCompleteCallback(callback) 

1335  

1336cdef CUresult cuGetExportTable(const void** ppExportTable, const CUuuid* pExportTableId) except ?CUDA_ERROR_NOT_FOUND nogil: 

1337 return cydriver._cuGetExportTable(ppExportTable, pExportTableId) 

1338  

1339cdef CUresult cuGreenCtxCreate(CUgreenCtx* phCtx, CUdevResourceDesc desc, CUdevice dev, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1340 return cydriver._cuGreenCtxCreate(phCtx, desc, dev, flags) 

1341  

1342cdef CUresult cuGreenCtxDestroy(CUgreenCtx hCtx) except ?CUDA_ERROR_NOT_FOUND nogil: 

1343 return cydriver._cuGreenCtxDestroy(hCtx) 

1344  

1345cdef CUresult cuCtxFromGreenCtx(CUcontext* pContext, CUgreenCtx hCtx) except ?CUDA_ERROR_NOT_FOUND nogil: 

1346 return cydriver._cuCtxFromGreenCtx(pContext, hCtx) 

1347  

1348cdef CUresult cuDeviceGetDevResource(CUdevice device, CUdevResource* resource, CUdevResourceType typename) except ?CUDA_ERROR_NOT_FOUND nogil: 

1349 return cydriver._cuDeviceGetDevResource(device, resource, typename) 2-W

1350  

1351cdef CUresult cuCtxGetDevResource(CUcontext hCtx, CUdevResource* resource, CUdevResourceType typename) except ?CUDA_ERROR_NOT_FOUND nogil: 

1352 return cydriver._cuCtxGetDevResource(hCtx, resource, typename) 

1353  

1354cdef CUresult cuGreenCtxGetDevResource(CUgreenCtx hCtx, CUdevResource* resource, CUdevResourceType typename) except ?CUDA_ERROR_NOT_FOUND nogil: 

1355 return cydriver._cuGreenCtxGetDevResource(hCtx, resource, typename) 

1356  

1357cdef CUresult cuDevSmResourceSplitByCount(CUdevResource* result, unsigned int* nbGroups, const CUdevResource* input, CUdevResource* remainder, unsigned int flags, unsigned int minCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

1358 return cydriver._cuDevSmResourceSplitByCount(result, nbGroups, input, remainder, flags, minCount) 2-W

1359  

1360cdef CUresult cuDevSmResourceSplit(CUdevResource* result, unsigned int nbGroups, const CUdevResource* input, CUdevResource* remainder, unsigned int flags, CU_DEV_SM_RESOURCE_GROUP_PARAMS* groupParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1361 return cydriver._cuDevSmResourceSplit(result, nbGroups, input, remainder, flags, groupParams) 

1362  

1363cdef CUresult cuDevResourceGenerateDesc(CUdevResourceDesc* phDesc, CUdevResource* resources, unsigned int nbResources) except ?CUDA_ERROR_NOT_FOUND nogil: 

1364 return cydriver._cuDevResourceGenerateDesc(phDesc, resources, nbResources) 

1365  

1366cdef CUresult cuGreenCtxRecordEvent(CUgreenCtx hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil: 

1367 return cydriver._cuGreenCtxRecordEvent(hCtx, hEvent) 

1368  

1369cdef CUresult cuGreenCtxWaitEvent(CUgreenCtx hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil: 

1370 return cydriver._cuGreenCtxWaitEvent(hCtx, hEvent) 

1371  

1372cdef CUresult cuStreamGetGreenCtx(CUstream hStream, CUgreenCtx* phCtx) except ?CUDA_ERROR_NOT_FOUND nogil: 

1373 return cydriver._cuStreamGetGreenCtx(hStream, phCtx) 

1374  

1375cdef CUresult cuGreenCtxStreamCreate(CUstream* phStream, CUgreenCtx greenCtx, unsigned int flags, int priority) except ?CUDA_ERROR_NOT_FOUND nogil: 

1376 return cydriver._cuGreenCtxStreamCreate(phStream, greenCtx, flags, priority) 

1377  

1378cdef CUresult cuGreenCtxGetId(CUgreenCtx greenCtx, unsigned long long* greenCtxId) except ?CUDA_ERROR_NOT_FOUND nogil: 

1379 return cydriver._cuGreenCtxGetId(greenCtx, greenCtxId) 

1380  

1381cdef CUresult cuStreamGetDevResource(CUstream hStream, CUdevResource* resource, CUdevResourceType typename) except ?CUDA_ERROR_NOT_FOUND nogil: 

1382 return cydriver._cuStreamGetDevResource(hStream, resource, typename) 

1383  

1384cdef CUresult cuLogsRegisterCallback(CUlogsCallback callbackFunc, void* userData, CUlogsCallbackHandle* callback_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

1385 return cydriver._cuLogsRegisterCallback(callbackFunc, userData, callback_out) 

1386  

1387cdef CUresult cuLogsUnregisterCallback(CUlogsCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil: 

1388 return cydriver._cuLogsUnregisterCallback(callback) 

1389  

1390cdef CUresult cuLogsCurrent(CUlogIterator* iterator_out, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1391 return cydriver._cuLogsCurrent(iterator_out, flags) 

1392  

1393cdef CUresult cuLogsDumpToFile(CUlogIterator* iterator, const char* pathToFile, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1394 return cydriver._cuLogsDumpToFile(iterator, pathToFile, flags) 

1395  

1396cdef CUresult cuLogsDumpToMemory(CUlogIterator* iterator, char* buffer, size_t* size, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1397 return cydriver._cuLogsDumpToMemory(iterator, buffer, size, flags) 

1398  

1399cdef CUresult cuCheckpointProcessGetRestoreThreadId(int pid, int* tid) except ?CUDA_ERROR_NOT_FOUND nogil: 

1400 return cydriver._cuCheckpointProcessGetRestoreThreadId(pid, tid) 

1401  

1402cdef CUresult cuCheckpointProcessGetState(int pid, CUprocessState* state) except ?CUDA_ERROR_NOT_FOUND nogil: 

1403 return cydriver._cuCheckpointProcessGetState(pid, state) 2+0

1404  

1405cdef CUresult cuCheckpointProcessLock(int pid, CUcheckpointLockArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil: 

1406 return cydriver._cuCheckpointProcessLock(pid, args) 

1407  

1408cdef CUresult cuCheckpointProcessCheckpoint(int pid, CUcheckpointCheckpointArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil: 

1409 return cydriver._cuCheckpointProcessCheckpoint(pid, args) 

1410  

1411cdef CUresult cuCheckpointProcessRestore(int pid, CUcheckpointRestoreArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil: 

1412 return cydriver._cuCheckpointProcessRestore(pid, args) 

1413  

1414cdef CUresult cuCheckpointProcessUnlock(int pid, CUcheckpointUnlockArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil: 

1415 return cydriver._cuCheckpointProcessUnlock(pid, args) 

1416  

1417cdef CUresult cuProfilerStart() except ?CUDA_ERROR_NOT_FOUND nogil: 

1418 return cydriver._cuProfilerStart() 2.W

1419  

1420cdef CUresult cuProfilerStop() except ?CUDA_ERROR_NOT_FOUND nogil: 

1421 return cydriver._cuProfilerStop() 2.W

1422  

1423cdef CUresult cuGraphicsEGLRegisterImage(CUgraphicsResource* pCudaResource, EGLImageKHR image, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1424 return cydriver._cuGraphicsEGLRegisterImage(pCudaResource, image, flags) 

1425  

1426cdef CUresult cuEGLStreamConsumerConnect(CUeglStreamConnection* conn, EGLStreamKHR stream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1427 return cydriver._cuEGLStreamConsumerConnect(conn, stream) 

1428  

1429cdef CUresult cuEGLStreamConsumerConnectWithFlags(CUeglStreamConnection* conn, EGLStreamKHR stream, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1430 return cydriver._cuEGLStreamConsumerConnectWithFlags(conn, stream, flags) 

1431  

1432cdef CUresult cuEGLStreamConsumerDisconnect(CUeglStreamConnection* conn) except ?CUDA_ERROR_NOT_FOUND nogil: 

1433 return cydriver._cuEGLStreamConsumerDisconnect(conn) 

1434  

1435cdef CUresult cuEGLStreamConsumerAcquireFrame(CUeglStreamConnection* conn, CUgraphicsResource* pCudaResource, CUstream* pStream, unsigned int timeout) except ?CUDA_ERROR_NOT_FOUND nogil: 

1436 return cydriver._cuEGLStreamConsumerAcquireFrame(conn, pCudaResource, pStream, timeout) 

1437  

1438cdef CUresult cuEGLStreamConsumerReleaseFrame(CUeglStreamConnection* conn, CUgraphicsResource pCudaResource, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1439 return cydriver._cuEGLStreamConsumerReleaseFrame(conn, pCudaResource, pStream) 

1440  

1441cdef CUresult cuEGLStreamProducerConnect(CUeglStreamConnection* conn, EGLStreamKHR stream, EGLint width, EGLint height) except ?CUDA_ERROR_NOT_FOUND nogil: 

1442 return cydriver._cuEGLStreamProducerConnect(conn, stream, width, height) 

1443  

1444cdef CUresult cuEGLStreamProducerDisconnect(CUeglStreamConnection* conn) except ?CUDA_ERROR_NOT_FOUND nogil: 

1445 return cydriver._cuEGLStreamProducerDisconnect(conn) 

1446  

1447cdef CUresult cuEGLStreamProducerPresentFrame(CUeglStreamConnection* conn, CUeglFrame eglframe, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1448 return cydriver._cuEGLStreamProducerPresentFrame(conn, eglframe, pStream) 

1449  

1450cdef CUresult cuEGLStreamProducerReturnFrame(CUeglStreamConnection* conn, CUeglFrame* eglframe, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1451 return cydriver._cuEGLStreamProducerReturnFrame(conn, eglframe, pStream) 

1452  

1453cdef CUresult cuGraphicsResourceGetMappedEglFrame(CUeglFrame* eglFrame, CUgraphicsResource resource, unsigned int index, unsigned int mipLevel) except ?CUDA_ERROR_NOT_FOUND nogil: 

1454 return cydriver._cuGraphicsResourceGetMappedEglFrame(eglFrame, resource, index, mipLevel) 

1455  

1456cdef CUresult cuEventCreateFromEGLSync(CUevent* phEvent, EGLSyncKHR eglSync, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1457 return cydriver._cuEventCreateFromEGLSync(phEvent, eglSync, flags) 

1458  

1459cdef CUresult cuGraphicsGLRegisterBuffer(CUgraphicsResource* pCudaResource, GLuint buffer, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1460 return cydriver._cuGraphicsGLRegisterBuffer(pCudaResource, buffer, Flags) 24g2o5g6g3o9W!W#W$W%W7g8g9g1i!gqr#g(W$g9kGh)W*W+W

1461  

1462cdef CUresult cuGraphicsGLRegisterImage(CUgraphicsResource* pCudaResource, GLuint image, GLenum target, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1463 return cydriver._cuGraphicsGLRegisterImage(pCudaResource, image, target, Flags) 2'W

1464  

1465cdef CUresult cuGLGetDevices(unsigned int* pCudaDeviceCount, CUdevice* pCudaDevices, unsigned int cudaDeviceCount, CUGLDeviceList deviceList) except ?CUDA_ERROR_NOT_FOUND nogil: 

1466 return cydriver._cuGLGetDevices_v2(pCudaDeviceCount, pCudaDevices, cudaDeviceCount, deviceList) 

1467  

1468cdef CUresult cuVDPAUGetDevice(CUdevice* pDevice, VdpDevice vdpDevice, VdpGetProcAddress* vdpGetProcAddress) except ?CUDA_ERROR_NOT_FOUND nogil: 

1469 return cydriver._cuVDPAUGetDevice(pDevice, vdpDevice, vdpGetProcAddress) 

1470  

1471cdef CUresult cuVDPAUCtxCreate(CUcontext* pCtx, unsigned int flags, CUdevice device, VdpDevice vdpDevice, VdpGetProcAddress* vdpGetProcAddress) except ?CUDA_ERROR_NOT_FOUND nogil: 

1472 return cydriver._cuVDPAUCtxCreate_v2(pCtx, flags, device, vdpDevice, vdpGetProcAddress) 

1473  

1474cdef CUresult cuGraphicsVDPAURegisterVideoSurface(CUgraphicsResource* pCudaResource, VdpVideoSurface vdpSurface, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1475 return cydriver._cuGraphicsVDPAURegisterVideoSurface(pCudaResource, vdpSurface, flags) 

1476  

1477cdef CUresult cuGraphicsVDPAURegisterOutputSurface(CUgraphicsResource* pCudaResource, VdpOutputSurface vdpSurface, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1478 return cydriver._cuGraphicsVDPAURegisterOutputSurface(pCudaResource, vdpSurface, flags)