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

983 statements  

« prev     ^ index     » next       coverage.py v7.14.0, created at 2026-05-22 01:37 +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) 2;Ley=L

9  

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

11 return cydriver._cuGetErrorName(error, pStr) 2,rtl-rulvl=bwl;Ley=L(Y~ abBh

12  

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

14 return cydriver._cuInit(Flags) 2a ;pfy.rgyhyiyjykylymynyoypyqyrysytyuyvy/r:r;r=r?r@r[r]r^r_r`r{r|r}r~rasbscsdsesfsgshsisjsks=plswyxyyyzyAyByCyDyEyFyGyHyIyJyKyLyMy)YNyOy

15  

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

17 return cydriver._cuDriverGetVersion(driverVersion) 2a *Y+Y,Y-Y.Y/Y

18  

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

20 return cydriver._cuDeviceGet(device, ordinal) 2fygyhyiyjykylymynyoypyqyrysytyeyuyvy/r:r;r=r?r@r[r]r^r_r`r{r|r}r~rasbscsdsesfsgshsisjsks=plswyxyyyzyAyByCyDyEyFyGyHyIyJyKyLyMyNyOy

21  

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

23 return cydriver._cuDeviceGetCount(count) 2a ?L@L[L]L^L_L`L{L|L}L~LaMbMcMdMeMfMgMhMiMjMkMlMmMnMoMpMqMrMsMtMuMvMPyQyRySy:YTyUyVyWyXyxl]iylYy^izlAlZy0y1y2ywM3y4y5y6y7y8y9y!y#y$y%y'y(y)y*y+y,y-y.y/y:y;y=y?y@y[y]y^y_y`y{y|y}y~yazBlCl?b_i{d|d`iDlElFlGlod}dChDhEhFhHlIlJlKl@b{i~dae|iLlMlNlOlpdbeGhHhIhJhPlQlRl}iSlbz~iTlUlVlajWlbjXlYlZl0l[bcjcededj1l2l3l4lqdeeKhLhMhNh5l6l7l8l]bejfegefj9l!l#l$lrdheOhPhQhRh%l'l(l)l^bgjiejehj*l+l,l-lsdkeShThUhVh.l/l:l;l_bijlemejj=l?l@l[ltdneWhXhYhZh]l^l_lkj`llj{l|l}lmj~lnjambmxMcmojdmpjemfmyMzMAMBMCMDMEMFMGMHMIMJMKMLMMMNMOMPMQMRMSMTMUMVMWMXMYMZM0M1M2M3M4M5M6M7M8M9M!M#M$M%M'M(M)M*M+M,M0 -M.M/M:M;M=M?M@M[M]M^M_M`M{Mcz|M}M~MaNbNcNdNeN?pfNms@pgm[p]p^p_p`pgNhmqjnsimrjjmsjos{p|p}p~paqbqcqdqeqhNiNdztjezfzgzfqhzizoejzpekz' A qe`begudlzmznzozpzqzrzszkmtzuzvzwzxzyzzzAzBzCzDzEzFzGzHzIzJzKzgqreSbbbcb- ;pTbdbse0hteebfbgbhbpsibjb.rjNkNlNmNnNoNqsrssstsusvswsxsyszsAsBsCsDsEsLz1 RcpNlmqNrNsNtNuNvNwNxNyNzNANBNMzujvjuemmnmwjxjyjCNzjAjBjNzOzPzQzRzSzTzUzVzWzXzYzZz0z1z2z3z4zDNScTcUcVcWcFsGsHsIsJsKsLsMsNsOsPsQsRsSsTsUsVsWsXsYsZs0s1s2s3s4s5s6s7s8s9s!s#s$s%s's{bomfghqiqjq(s)s*s+s,s-s.s/s:s;s=s?s@s[s]s^s_s`s{s|s}s~satbtctdtetftgthtitjtktltmtntotUbXcEN1hFN2h3hGNkbHNvdIN4hJNveKNwd|bLN5hMNweCjxe6hye7hNNzeONxd}b8hAeggPNydhgQNigRNjgkgSNYclg9hTNBezd~b!hCeUNDjDe#hEeVN$hWNFeXNAdacYN%hGeZNmg0Nng'h1NBdZcCd2NEj5zpmHeVb3NbcIekq(h)h~ ab;Y4Nqmrm5Nsm6Ntmumvm7NwmBh8N9N!N#N$N%N'N(N)N*NxmymptqtrtstttutzmAmBmCmDmEmFmGmHmImJmKmLmMmNmOmPmQmRmSmTmUmVmWmXmYmZm0m1m2m3m4m5m6m7m8m9m!m#m$m%m'm(m)m*m+m,m-m.m/m:m;m=m?m@m[m]m^m_m`m{m|m}m~manbnvtcndnenFjcclq+N,NGj6zHjIjJj7zfngnhninJeKe*hmq8zwtjnknKjlnxtmnLjdcnq-N9zMj!zNjOjPj#znnonpnqnLeMe+hoq$zytrnsnWbNeOeQjogpgqgDdPe,hrgsgQe( ReEd0c1cFd-hGdHdIdSeXbRjYb2ctg.hJdKdlbmbZb. / : ; /hnbugvgwgxg:htnun3cLdygpqvnwnxnSjecqqTjUjVjWj%zynznAnBnTe.NUe;hrq'zCnDnXj=h0bEn(z?hzt@h[h]hAtYjZj0j1jMd)zNdzgFnBtsq2j3j4jobOdPd^hVeWeXe4cYeAgZe0e5j_h1bGn*z`h6j7j{hCt8j9j!j#jQd+zRdBgHnDt$j%j|h}h1e2e3e4e~h5e6e7e8epbSdTd9e!eUdCg#e$eInfctq'j(j)j*jJnKnLn%e'eai,zMnNnDgEgFgGgOnPnQnRnSnbigcHgIgVdWdJg+j(e)e*e+e5c,e,j-e.ehc6c7c8cXdicjcqbkclcmcTnncuq-j.j/j:j-zUnVnWnXn/e:ecivq.zYnZn5 2b3boc9c!c#c$c= %c'cYd;e=eZd?e@e;jpcdiei[e]efi0nKgLgMg1n^e0dNg2nOgPg3nqc=j?j@j[j4n5n6n_e`egi7n8nhiQgrb]jEtRgwqSgTgUgxqiijikili(cFt)c{e^jyqmini9n!n_jrczq/N:N`j/z{j|j}j:z#n$n%n'n|e}eoiAq;zGt(n)n4b~eaf~jVgWgXg1dbfpiYgZgcf) df2d*c+c3dqi4d5d6def5bak6b,crisi7d8dsbtb7b? @ [ ] tiub0g1g2g3gui*n+n-c9d4gBq,n-n.nbkscCqckdkekfk=z/n:n;n=nff;NgfviHt?z?n@n[ngktcDq=Nhk@zikjkkk[z]n^n_n`nhf?NifwiIt]zJt{n|nlkvb!d#dxijfkflf.cmf5gnfofmkyi8b}n^zzinkokAiKtpkqkrksk$d_z%d6gEqLttkukBiCipfqfrfsfDitfufvfwfwb'd(dxfyfzf)d7gAfBf~nucFqvkwkxkykaobocoCfDfEi`zdoeo8g9g!g#gfogohoiojoFivc$g%g*d+d'gzkEfFfGfHf/cIfAkJfKfwc:c;c=c,dxcycxbzcAcBckoCcGqBkCkDkEk{zlomonoooLfMfGiMt|zpoqo6 9b!bDc?c@c[c]c^ ^c_c-dNfOf.dPfQfroEcFkGk(g)gHkHqHiIiJisoRfSfKiIqLiMitoFcIkJkKkLkuovowoTfUfNixoyoOi*gybMkNt+gJq,g-g.gKqPiQiRiSi`cOt{cVfzoLqTiUiAo@N[N|c}c/d:dPtQtBoNkGcMq]N}zOk~zPkQkRkaACoDoEoFoWfXfViNqOqPqRtStTtbAUtGoHoIoSkHcQq^N_NTkcAUkVkWkdAJoKoLoMoYfZfWiRqeAVtNoOoPoXkIcSq`NfAYkgAZk0k1khAQoRoSoTo0f1fXiTqiAWtUoVoWo2kJcUq{NjA3kkA4k5k6klAXoYoZo2f3fYiVqmAXt0o1o2o7kKcWq|NnA8koA9k!k#kpA3o4o5o6o4f5fZiXqqAYt7o8o9o$kLcYq}NrA%ksA'k(k)ktA!o#o$o6f7f0iZquAZt%o'o(o*kMc0q~NaO+kvA,k-k.kwA)o*o+o,o8f9f1i0t1txA-o.o/o/kNc1qbOcO:kyA;k=k?kzA:o;o=o?o!f#f2i2t3tAA4t@o[odOeO5tfOgOhOiOjOkOlOmOnOoOpOqOrOsOtOuOvOwOxOyOzOAOBOCODOEOFOGOHOIOJOKO6t7t8t]oLOMONOOOPOQOROSOTO9t!t#t$t%tUO't(t)t*t+tVOWOXOYOZO0O1O2O3O4O5O6O7O8O9O!O#O$O%O'O(O)O*O+O,O-O.O/O:O;O=O?O@O[O]O,t-t.t/t:t;t=t?t@t[t]t^t_t`t{t|t}t~taubucudueufuguhuiujukulumunuoupuqurusutu^O_O`Ouuvuwu{O|O}O~OaPbPcPdPePfPgPhPiPjPkPlPmP$f%f'f(f)f*f+f,f-f.f/f:f;f=f?f@f[f]f^f_f`fnPoPpPqPrPsPtPuPvPwPxPyPzPAPBPCPDPEPFPGPHPIP

24  

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

26 return cydriver._cuDeviceGetName(name, length, dev) 2gmiN=Y^o_ofqxuoepe' A `oqe{o|o}o3i~o`begudgqyuzuAureBuSb4ibbcb- {fTbdbse0hteCu.rJPBA}z

27  

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

29 return cydriver._cuDeviceGetUuid_v2(uuid, dev) 2gm]ptjkm;pappsjN?Y@Y[Y]Y^YCADAve|bwexeyeze}bAeBe~bCeDeEeFeacGemgbc(h)hvt9zXj=h0bEn(z?hzt@h[h]hAtYjZj0j1jMd)zNdzgFnBtsq2j3j|c}c/d:dfAjAnArA

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 S T 7 2 * zbc d e f g h i j k l m n o p q r s t u v H I J K EAFA2q,rDuGAEuxl]iyl^izlAl3q~cadbd;d3 _Y`YAbBbCb#bDb8 9 ! + $b%b'bOc{Y4q5q6q7q8q9q5i@kBlCl?b_i{d|d`iod}dChDhEhFhJlKl@b{i~dae|ipdbeGhHhIhJhRl}iSl~iTlUlVlajWlbjXlYlZl0l[bcjcededjqdeeKhLhMhNh7l8l]bejfegefjrdheOhPhQhRh(l)l^bgjiejehjsdkeShThUhVh:l;l_bijlemejjtdneWhXhYhZh_lkj`llj{l|l}lmj~lnjambmcmojdmpjemfm|Y[k!q=d}Ycd~YKPLPMPNPOPEbFbGbHb(b?d@dL N #q|fX _ ` )bO M B C D b w czG Y Z Ib*b+bddU ?pFu@p[p^p_p`p$qhmqjnsimrjjmsjos{p|p}p~paqbqcqdqeqtj' A km%q'q(q;papps.rbpHAIA/g:gJAKALAMANAOAPAQARAqsSATAUAVArsWAXAYAsstsZA0A1A2A3A4A5A6A7A8A9A!Aus#A$APP%A'A(A)A*A+A,A-AQP.A/A:A;A=A?A@A[A]A^A_A`A{A|ARP}A~AaBSPvsbBcBwsdBeBfBTPgBhBiBjBkBlBmBnBxsoBpBqBrBsBtBuBvBwBxByBzBABBBysCBDBEBFBGBzsHBIBAsJBKBLBMBNBOBPBQBRBSBTBUBVBBsUPWBXBYBCsZB0B1B2B3B4B5B6B7BDs8B9B!B#B$B%B'B(B)B1 { PcJbueV mmW nmaZbZKb[d]d6i7i8i}f9i!i^dScTcUcVcWcFsGsHsIsJsKsLsMsNsOsPsQsRsSsTsUsVsWsXsYsZs0s1s2s3s4s5s6s7s8s9s!s#s$s%s's;gfg#i$iUb]kXcGu^kHu1h2h3hIukb%ivd_k4hvewd|b5hwexe6hye7hzexd}b8hAegg*B+Bhg,Big-Bjg.Bkg/BYc:Blg;B9hBezd~b!hCeDe#hEe$hFeAdac%hGemgng'hBdZcCd5z=gHe`kVbbcIe(h)hVPedfd~ abgd=BJuqmrm)qsm*qtmumvm4 wmBh+q,q-q.q/q:q;q=q?q@qxmymptqtrtstttut?Bzm@BAm[BBm]BCm^BDm_BEmKuFmLuGmMuHmNuImOuJmPuKmQuLmRuMmSuNmTuOmUuPmVuQmWuRmXuSmYuTmZuUm0uVm1uWmXmYm`BZm{B0m|B1m}B2m~B3maC4mbC5mcC6mdC7meC8mfC9mgC!mhC#miC$mjC%mkC'mlC(mmC)mnC*moC+mpC,m-m.m[q/m:m;m=m?m@m[m]m^m_m`m{m|m}m~mvtenFjccGjJjinJeKe*hmqKjlnmnLjdcMjPjqnLeMe+hoqWbNeOeQjogpgqgDdPe,hrgsgQe( ReEd0c1cFd-hGdHdIdSeXbRjYb2ctg.hJdKdlbmbZb. / : ; /hnbugxg3cLdygxnSjecTjWjBnTeUe;hrqXj=h0b?h]h1jMdNdzgFn4jobOdPd^hVeWeXe4cYeAgZe0e5j_h1b`h{h#jQdRdBgHnpbSdTd9e!eUdCg#e$eInfc'j*j%e'eaibigcHgIgVdWdJg+j(e)e*e+e5c,e,j-e.ehc6c7c8cXdicjcqbkclcmcTnnc-j:jXn/e:ecivq5 2b3boc9c!c#c$c= %c'cYd;e=eZd?e@e;jpcdiei[e]efi0nKgLgMg1n^e0dNg2nOgPg3nqc=j[j_e`egihiQgrbRgUgli(c)c{e^j!n_jrc`j}j'n|e}eoiAq4b~eaf~jVgWgXg1dbfpiYgZgcf) df2d*c+c3dqi4d5d6def5bak6b,crisi7d8dsbtb7b? @ [ ] tiub0g3g-c9d4g.nbkscckfk=nffgfviHt[ngktchkkk`nhfifwiItlkvb!d#dxijfkflf.cmf5gnfofmkyi8bziAisk$d%d6gEqwb'd(dxfyfzf)d7gAfBf~nucvkykCfDfEiFivc$g%g*d+d'gzkEfFfGfHf/cIfAkJfKfwc:c;c=c,dxcycxbzcAcBckoCcBkEkooLfMfGiMt6 9b!bDc?c@c[c]c^ ^c_c-dNfOf.dPfQfroEcFkGk(g)gHkHqHiIiJisoRfSfKiIqLiMitoFcIkLkTfUfNiOi*gyb+g.gSi`c{cVfzo|c}c/d:dPtQtBoNkGcOkRkFoWfXfViNqOqPqRtStTtIoSkHcTkWkMoYfZfWiRqPoXkIcYk1kTo0f1fXiTqWo2kJc3k6kZo2f3fYiVq2o7kKc8k#k6o4f5fZiXq9o$kLc%k)k$o6f7f0iZq(o*kMc+k.k,o8f9f1i0t1t/o/kNc:k?k?o!f#f2i2t3tWPXP5tYPZP6t7t8t]o9t!t#t$t%t2u't(t)t*t+t3u,t-t.t/t:t;t=t?t@t[t]t^t_t`t{t|t}t~taubucudueufuguhuiujukulumunuoupuqurusutuuuvuwu$f%f'f(f)f*f+f,f-f.f/f:f;f=f?f@f[f]f^f_f`fcp

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) 20P

51  

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

53 return cydriver._cuDeviceGetMemPool(pool, dev) 2L N ,b-b.bx , y z E | w F /g:gJbV W ;gfg#i$i%i=g4 FjKjLjQe( ReEd0c1cFd-hGdHdIdSeXbRjYb2ctg.hJdKdSj=h_hQg_jcf) df2d*c+c3dqi4d5d6def5bak6b,crisi7d8dbkgkyi*gNkSkXk2k7k$k*k/k$f%f'f(f)f*f+f,f-f.f/f:f;f=f?f@f[f]f^f_f`fcp

54  

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

56 return cydriver._cuDeviceGetDefaultMemPool(pool_out, dev) 20P

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) 21P/r:r;r=r?r@r[r]r^r_r`r{r|r}r~rasbscsdsesfsgshsisjsks=pls

72  

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

74 return cydriver._cuDevicePrimaryCtxRelease_v2(dev) 2cZdZeZfZgZhZiZjZkZlZmZnZoZpZqZrZsZtZuZvZwZxZyZzZAZBZ=pCZDZ

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) 2fygyhyiyjykylymynyoypyqyrysytyuyvywyxyyyzyAyByCyDyEyFyGyHyIyJyKyLyMyNyOy

87  

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

89 return cydriver._cuCtxDestroy_v2(ctx) 2EZFZGZHZIZJZKZLZMZNZOZPZQZRZSZTZUZVZWZXZYZZZ0Z1Z2Z3Z4Z5Z6Z7Z8Z9Z!Z#Z$Z

90  

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

92 return cydriver._cuCtxPushCurrent_v2(ctx) 2qC2P

93  

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

95 return cydriver._cuCtxPopCurrent_v2(pctx) 23P4P5P6P7P8P9P!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~PrCsCtCuCvCwCxCyCzCACBCCCDCECFCGCHCICJCKCLCaQMCNCOCPCQC4uRCSCbQcQTCUCVCWCXCYCZC0C1C2C3C4C5CdQ6C7C8C9C!C#C$C%C'C(C)C*C+C,CeQ5u6u-C.CfQ/C:C;C=C?C@C[C]C^C_C`C{C|CgQ7u8u}C~ChQaDbDcDdDeDfDgDhDiDjDkDlDmDnDoDpDqDrDsDtDuDvDwDxDyDzDAD9u!uBDCDDDEDFDGDHDIDJDKDLDMDNDODPDQDRD#u$uSDTDUDVDWDXDYDZD0D1D2D3D4D5D6D7D8D%u'u9D!D#D$D%D'D(D)D*D+D,D-D.D/D:D;D=D(u)u?D@D[D]D^D_D`D{D|D}D~DaEbEcEdEeEfEgEhEiEjEkElEmEnEiQoEpEqErEsEtEjQkQlQmQnQoQpQqQrQsQtQuQvQwQxQyQzQAQBQCQDQEQFQGQHQIQJQKQLQMQNQOQPQQQRQSQTQUQVQWQXQYQZQ0Q1Q2Q3Q4Q5Q6Q7Q8Q9Q!Q#Q$Q%Q'Q(Q)Q*Q+Q,Q-Q.Q/Q:Q;Q=Q?Q@Q[Q]Q^Q_Q`QuEvEwExE{Q|QyEzE}QAEBECEDE~QEEFEaRbRcRdReRfRgRhRiRjRkRlRmRnRoRpRqRrRsRtRuRvRwRxRyRzRARBRCRDRERFRGRHRIRJRKRLRMRNRORPRQRRRSRTRURVRWRGEHEIEXRYRqCJEKELEZRME2PNEOE0R1R2R3R4R5R6R7R8R9R!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~RaSbScSdSeSfSgShSiSjSkSlSmSnSoSpSqSrSsStSuSvSwSxSySzSASBSCSDSESFSGSHSISJSKSLSMSNSOSPSQSRSSSTSUSVSWSXSYSZS0S1S2S3S4S5S6S7S8S9S!S#S$S%S'S(S)S*S+S,S-S.S/S:S;S=S?S@S[S]S^S_S`S{S|S}S~SaTbTcTdTeTfTgThTiTjTkTlTmTnToTpTqTrTsTtTuTvTwTxTyTzTATBTCTDTETFTGTHTITJTKTLTMTNTOTPTQTRTSTTTUTVTWTXTYTZT0T1T2T3T4T5T6T7T8T9T!T#T$T%T'T(T)T*T+T,T-T.T/T:T;T=T?T@T[T]T^T_T`T{T|T}T~TaUbUcUdUeUfUgUhUiUjUkUlUPEQERESEmUnUTEUE*u+uVEWEXEYEZEoU0E1E2EpU3E4E5E6E7EqU8E9E!E#E$ErUsU%E'E,u-u(E)E*E+E,EtU-E.E/EuU:E;E=E?E@E.u/u[E]E^E_E`E{E|E}E~E:u;u=u?u]q^q@u[u]u^u_uaF`ubF{u|ucF}u~uavbvcvdFeFfFgFhFiFjFkFdvevlFmFnFoFpFqFrFsFtFuFvFwFxFyFzFfvgvAFBFCFDFEFvUFFwUGFHFxUIFJFKFLFMFNFOFyUPFQFhvivRFSFTFUFVFzUWFAUXFYFBUZF0F1F2F3F4Fjvkv5F6F7F8F9F!F#F$F%Flvmvnvov'Fpvqvrvsvtvuvvvwv(Fxv)Fyvzv*FAvBvCvDvEvFvGvHvIvJvKvLvMvNv+FOvPv,F-F.F/F:F;F=F?F@F[F]FQvRv^F_F`F{F|F}F~FaGbGcGdGeGfGgGhGiGjGkGlGmGnGoGpGSvTvqGrGsGtGuGvGwGxGyGzGAGBGUvVvCGDGEGFGGGHGIGJGKGLGMGNGWvXvOGPGQGRGSGCUTGUGVGDUWGXGYGZGYvZv0G1G2G3G4G5G0v1v6G7G8G9G!G#G$G%G'G(G2v3v)G*G+G,G-GEU.G/G:G;G=G?G@G[G]G4v5v^G_G`G{G|G}G~GaHbH6v7v8v9vcH!v#v_q`q$v%v'v(v)vdH*veH+v,vfH-v.v/vgHhHiHjHkHFUGUlHmH:v;vnHoHpHqHrHHUsHtHuHIUvHwHxHyHzH=v?vAHBHCHDHEHFHGHHHIH@v[v]v^v{q|q_v`v{v|v}vJH~vKHawbwLHcwdwewfwgwMHNHOHPHQHRHSHTHhwiwUHVHWHXHYHZH0H1H2H3H4H5H6H7H8Hjwkw9H!H#H$H%HJU'HKU(H)HLU*H+H,H-H.H/H:HMU;H=Hlwmw?H@H[H]H^HNU_HOU`H{HPU|H}H~HaIbIcInwowdIeIfIgIhIiIjIkIlIpwqwrwswmItwuwvwwwxwywzwAwnIBwoICwDwpIEwFwGwHwIwJwKwLwMwNwOwPwQwRwqISwTwrIsItIuIvIwIxIyIzIAIBIUwVwCIDIEIFIGIHIIIJIKILIMINIOIPIQIRISITIUIVIWIXIYIWwXwZI0I1I2I3I4I5I6I7I8I9I!IYwZw#I$I%I'I(I)I*I+I,I-I.I/I0w1w:I;I=I?I@IQU[I]I^IRU_I`I{I|I2w3w}I~IaJbJcJdJ4w5weJfJgJhJiJjJkJlJmJnJ6w7woJpJqJrJsJSUtJuJvJwJxJyJzJAJBJ8w9wCJDJEJFJGJHJIJJJKJ!w#w$w%wLJ'w(w}q~q)w*w+w,w-wMJ.wNJ/w:wOJ;w=w?wPJTUUUVUWUQJRJSJTJXUYUUJVJ@w[wWJXJYJZJ0JZU1J2J3J0U1U2U3U4U5U4J5J6J7J8J9J!J#J6U7U$J%J]w^w'J(J)J*J+J8U,J-J.J9U/J:J;J=J?J@J[J]J!U#U^J_J_w`w`J{J|J}J~J$UaKbKcK%UdKeKfKgKhKiKjKkK'U(UlKmK{w|wnKoKpKqKrK)UsKtKuK*UvKwKxKyKzKAKBKCK+U,UDKEK}w~wFKGKHKIKJK-UKKLKMK.UNKOKPKQKRKSKTKUK/U:UVKWKaxbxXKYKZK0K1K;U2K3K4K=U5K6K7K8K9K!K#K$K?U@U%K'Kcxdx(K)K*K+K,K[U-K.K/K]U^U:K;K=K?K@K[K]K^K_U`U_K`Kexfx{K|K}K~KaL{UbLcLdL|U}UeLfLgLhL~UaVbVcVdVeVfVgVhViVjVkVlVmVnVoVpVqVrVsVtVuVvVwVxVyVzVAVBVCVDVEVFVGVHVIVJVKVLVMVNVOVPVQVRVSVTVUVVVWVXVYVZV0V1V2V3V4V5V6V7V8V9V!V#V$V%V'V(V)V*V+V,V-V.V/V:V;V=V?V@V[V]V^V_V`V{V|V}V~VaWbWcWdWeWfWgWhWiWjWkWlWmWnWoWpWqWrWsWtWuWvWwWxWyWzWAWBWCWDWEWFWGWHWIWJWKWLWMWNWOWPWQWRWSWTWUWVWWWXWYWZW0W1W2W3W4W5W6W7W8W9W!W#W$W%W'W(W)W*W+W,W-W.W/W:W;W=W?W@W[W]W^W_W`W{W|W}W~WaXbXcXdXeXfXgXhXiXjXkXlXmXnXoXpXqXrXsXtXuX

96  

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

98 return cydriver._cuCtxSetCurrent(ctx) 2?L@L[L]L^L_L%Z`L{L|L}L~LaMbMcMdMeMfMgMhMiMjMkMlMmMnMoMpMqMrMsMtMuMvMPyQyRySyTyUyVyWyXyxl]iylYy^izlAlZy0y1yvX2ywM3y4y5y6y7y8y9y!y#y$y%y'y(y)y*y+y,y-y.y/y:y;y=y?y@y[y]y^y_y`y{y|y}y~yazBlCl?b_i{d|d`iDlElFlGlod}dChDhEhFhHlIlJlKl@b{i~dae|iLlMlNlOlpdbeGhHhIhJhPlQlRl}iSlbz~iTlUlVlajWlbjXlYlZl0l[bcjcededj1l2l3l4lqdeeKhLhMhNh5l6l7l8l]bejfegefj9l!l#l$lrdheOhPhQhRh%l'l(l)l^bgjiejehj*l+l,l-lsdkeShThUhVh.l/l:l;l_bijlemejj=l?l@l[ltdneWhXhYhZh]l^l_lkj`llj{l|l}lmj~lnjambmxMcmojdmpjemfmyMzMAMBMCMDMEMFMGMHMIMJMKMLMMMNMOMPM'ZQMRMSMTMUMVMWMXMYMZM0M1M2M3M4M5M6M7M8M9M!M#M$M%M'M(M)M*M+M,M(Z-M.M/M:M;M=M?M@M[M]M^M_M`M{M)Z*Z+Z,Z-Z.Z/Z:Z;Z=Z?Z@Zcz[Z]Z^Z_Z`Z{Z|Z}Z~Za0|M}M~MaNbNcNdNb0eN?pFufN@p[p^p_p`p$qgNhmqjnsimrjjmsjos{p|p}p~paqbqcqdqeq'ihNiLtjjLgxkLhxlLixmLjxc0d0e0f0g0h0i0j0k0l0m0egnLudkxoLlxpLqLrLsLtLuLkmvLwLxLyLzLmxnx%qoxpxqxrxsxtxuxvxwxALxxBLyxCLzxDL'qbbELcb(qn0;pFLapGLAxHLBxo0p0q0psr0s0kNlNmN1PnNoNt0/r:r;r=r?r@r[r]r^r_r`r{r|r}r~rasbscsdsesfsgshsisjsks=pls/g:gu0v0w0x0y0z0A0B0C0D0JPEsE0F0~f1 RcpNlmqNG0rNsNtNH0uNvNwNxNyNzNI0ANBNJ0?gdp@g[gep]g^g_g(i`g{g|g{kMzujvjuemmnmwjxjyjCNzjAjBjNzOzPzQzRzSzTzUzVzWzXzYzZz0z1z2z3z4zDNKb)i*i^dK0L0M0N0}g~gScahbhchdhehfhghhhihjhkhlhmhTcnhohphqhUcVcrhshthuhWcvhwhFsGsHsIsJsKsLsMsNsOsPsQsRsSsTsUsVsWsXsYsZs0s1s2s3s4s5s6s7s8s9s!s#s$s%s's|k_d{bomwXarbrCx;gfghqDxExiqjqFxxXyX(s)szXAX*s+s,sBX-sCX.sDXEX/s:s;sFX=sGXHX?s@sIXJXKXLXMXNXOXPX[s]sQX^sRX_s`sSXTXUX{s|sVXWXXXYXZX}s0X1X2X3X4X5X~s6X7Xat8X9X!X#Xbt$Xct%X'X(X)X*Xdt+Xet,Xftgt-X.Xht/Xit:Xjt;Xkt=Xlt?Xmt@X[X]X^X_Xnt`Xot}k#i$iUbO0P0]kXcGuQ0^kR0HuEN1hFN2hS03hGNIuT0kbU0%iHNvdIN_kV04hJNveKNwdW0|bLN5hMNweX0CjY0xeZ06h00ye107hNNzeONxd20}b308h40Ae50gg60PNyd7080hgQN90ig!0RNjg#0$0kgSN%0Yc'0(0lg)0*09hTNBe+0zd,0~b-0!h.0CeUNDj/0De:0#h;0EeVN$hWNFeXNAd=0acYN%h?0GeZNmg0Nng@0'h1NBd[0Zc]0Cd2N5zILGxpmfp=gHe`k^0Vb3NbcIe_0`0{0|0edfd~ abgd=B4Nqmrm5Nsm6Ntmumvm7Nwm8N9N!N#N$N%N'N(N)N*NHxxmymptqtrtstttutzmAmBmCmDmEmFmGmHmImJmKmLmMmNmOmPmQmRmSmTmUmVmWmXmYmZm0m1m2m3m4m5m6m7m8m9m!m#m$m%m'm(m)m*m+m,m-m.m[q/m:m;m=m?m@m[m]m^m_m`m{m|m}m~man}0bnvtcn~0+ia1dnb1enFjcclq+N,NGj6zHjIjJj7zfngnhninJeKe*hmq8zwtjnknKjlnxtmnLjdcnq-N9zMj!zNjOjPj#znnonpnqnLeMe+hoq$zytrnsnWbNeOeQjogpgqgDdPe,hrgsgQe( ReEd0c1cFd-hGdHdIdSeXbRjYb2ctg.hJdKdlbmbZb. / : ; /hnbugvgwgxg:htnun3cLdygpqvnwnxnSjecqqTjUjVjWj%zynznAnBnTe.NUe;hrq'zCnDnXj=h0bEn(z?hzt@h[h]hAtYjZj0j1jMd)zNdzgFnBtsq2j3j4jobOdPd^hVeWeXe4cYeAgZe0e5j_h1bGn*z`h6j7j{hCt8j9j!j#jQd+zRdBgHnDt$j%j|h}h1e2e3e4e~h5e6e7e8epbSdTd9e!e,iUdCg#e$eInfctq'j(j)j*jJnKnLn%e'eai,zMnNnDgEgFgGgOnPnQnRnSnbigcHgIgVdWdJg+j(e)e*e+e5c,e,j-e.ehc6c7c8cXdicjcqbkclcmcTnncuq-j.j/j:j-zUnVnWnXn/e:ecivq.zYnZn5 2b3boc9c!c#c$c= %c'cYd;e=eZd?e@e;jpcdiei[e]efi0nKgLgMg1n^e0dNg2nOgPg3nqc=j?j@j[j4n5n6n_e`egi7n8nhiQgrb]jEtRgwqSgTgUgxqiijikili(cFt)c{e^jyqmini9n!n_jrczq/N:N`j/z{j|j}j:z#n$n%n'n|e}eoiAq;zGt(n)n4b~eaf~jVgWgXg1dbfpiYgZgcf) df2d*c+c3dqi4d5d6def5bak6b,crisi7d8dsbtb7b? @ [ ] tiub0g1g2g3gui*n+n-c9d4gBq,n-n.nbkscCqckdkekfk=z/n:n;n=nff;NgfviHt?z?n@n[ngktcDq=Nhk@zikjkkk[z]n^n_n`nhf?NifwiIt]zJt{n|nlkvb!d#dxijfkflf.cmf5gnfofmkyi8b}n^zzinkokAiKtpkqkrksk$d_z%d6gEqLttkukBiCipfqfrfsfDitfufvfwfwb'd(dxfyfzf)d7gAfBf~nucFqvkwkxkykaobocoCfDfEi`zdoeo8g9g!g#gfogohoiojoFivc$g%g*d+d'gzkEfFfGfHf/cIfAkJfKfwc:c;c=c,dxcycxbzcAcBckoCcGqBkCkDkEk{zlomonoooLfMfGiMt|zpoqo6 9b!bDc?c@c[c]c^ ^c_c-dNfOf.dPfQfroEcFkGk(g)gHkHqHiIiJisoRfSfKiIqLiMitoFcIkJkKkLkuovowoTfUfNixoyoOi*gybMkNt+gJq,g-g.gKqPiQiRiSi`cOt{cVfzoLqTiUiAo@N[N|c}c/d:dPtQtBoNkGcMq]N}zOk~zPkQkRkaACoDoEoFoWfXfViNqOqPqRtStTtbAUtGoHoIoSkHcQq^N_NTkcAUkVkWkdAJoKoLoMoYfZfWiRqeAVtNoOoPoXkIcSq`NfAYkgAZk0k1khAQoRoSoTo0f1fXiTqiAWtUoVoWo2kJcUq{NjA3kkA4k5k6klAXoYocrZo2f3fYiVqmAXt0o1o2o7kKcWq|NnA8koA9k!k#kpA3o4o5o6o4f5fZiXqqAYt7o8o9o$kLcYq}NrA%ksA'k(k)ktAdr!o#o$o6f7f0iZquAZt%o'o(o*kMc0q~NaO+kvA,k-k.kwA)o*o+o,o8f9f1i0t1txAJL-o.o/o/kNc1qbOcO:kyA;k=k?kzA:o;o=o?o!f#f2i2t3tAA4t@o[odOeOfOgOc1hOd1iOjOkOlOmOnOe1oOpOqOrOsOf1tOuOg1vOwOxOyOzOAOBOCODOEOFOGOHOIOJOh1KOi1j1k1LOMONOOOPOl1m1n1QOo1ROp1SOTOUOq1VOKLWOXOYOZO0O1O2Or13O4O{X5O6O7O8O9O!O#O$O%O'O(O)O*O+O,O-O.O/O:O;Oer=O?O@O[O]O,t-t.t/t:t;t=t?t@t[t]t^t_t`t{t|t}t~taubucudueufuguhuiujukulumunuoupuqurusutu^O_O`Ouuvuwu{Os1|O}O~OaPt1bPcPu1dPv1ePw1x1fPy1gPhPz1iPjPkPlPmP$f%ffrgrhr'f(f)firjrkrlrmrnr*f+f,f-f.forprqr/f:f;f=f?f@f[frrsrtr]f^furvr_fwr`fnPoPpPA1qPrPB1C1D1sPtPuPvPwPE1F1xPG1H1yPzPI1APBPCPDPJ1K1EPFPL1M1GPHPIP

99  

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

101 return cydriver._cuCtxGetCurrent(pctx) 2a 3P4P5P6P7P8P9P!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~PrCsCtCuCvCIxwCxCyCzCACBCCCDCECFCGCHCICJCKCLCaQMCNCOCPCQC4uRCSCbQcQTCUCVCWCXC8 YC9 ZC! 0C+ 1C$b2C%b3C'b4COc5CdQ6C7C8C9C!C#C$C%C'C(C)C*C+C,CeQ5u6u-C.CfQFl/CGl:C;C}d=CCh?CDh@CEh[CFh]CHl^CIl_C`C{C|CgQ7u8u}C~ChQNlaDOlbDcDbedDGheDHhfDIhgDJhhDPliDQljDkDlDmDnDoDpDqDrDsDtDuDvDwDxDyDzDAD9u!uBDCDDD3lED4lFDGDeeHDKhIDLhJDMhKDNhLD5lMD6lNDODPDQDRD#u$uSDTDUD#lVD$lWDXDheYDOhZDPh0DQh1DRh2D%l3D'l4D5D6D7D8D%u'u9D!D#D,l$D-l%D'Dke(DSh)DTh*DUh+DVh,D.l-D/l.D/D:D;D=D(u)u?D@D[D@l]D[l^D_Dne`DWh{DXh|DYh}DZh~D]laE^lbEcEdEeEfEgEhEiEjEkElEmEnEiQoEpEqErEsEtEtljQkQlQmQnQJxoQpQqQrQsQtQuQvQwQulxQyQzQAQBQCQDQEQFQgpGQhpHQipIQjpJQEbKQFbLQGbMQHbNQOQPQQQRQSQTQUQVQWQXQYQZQ0Q1Q2Q3Q4Q5Q6Q-i7Q8Q9Q!Q#Q$Q%Q'Q(Q)Qb *Q+Q=b,Q-Q.Q/Q:Q;Q=Q?Q@Q[Q]Q^Q_Q`QuEvEwExE{Q|QyEzE}QAEBECEDE~QEEFEaRbRcRdReRfRgRhRiRjRkRlRmRnRoRHAIA/gpR:gqRrRsRtRuRvRwRxRyRzRAR|XJAKALAMANAOAPAQARAqsSATAUAVArsWAXAYAsstsZA0A1A2A3A4A5A6A7A8A9A!Aus#A$A%A'A(A)A*A+A,A-A.A/A:A;A=A?A@A[A]A^A_A`A{A|A}A~AaBvsbBcBwsdBeBfBgBhBiBjBkBlBmBnBxsoBpBqBrBsBtBuBvBwBxByBzBABBBysCBDBEBFBGBzsHBIBAsJBKBLBMBNBOBPBQBRBSBTBUBVBBsWBXBYBCsZB0B1B2B3B4B5B6B7BDs8B9B!B#B$B%B'B(B)BBREsCRDRERBALzCAN1DA1 RcFRlmGRHRIRJRKRLRMRNRORPRQRRRSRTRURVR~kWRGEHEIEV XRW YRqCJEKELEZRMENEOE0R1R2R3R4R5R6R7R8R9R!R#R$R%R'R(R)R*R+R,R-R.R/RScTcUcVcWc:R;R=R?R@R[R]R^R_R`R{R|R}R~RaSbScSdSeSfSgShSiSjSkSlSmSnSoSpSqSrSsStSuSvS{bom(s)s*s+s,s-s.s/s:s;s=s?s@s[s]s^s_s`s{s|s}s~satbtctdtetftgthtitjtktltmtntotwSxSySzSASBSCSDSESFSGSHSISJSKSLSMSNSOSPSQSRSSSTSUSVSWSXSYSZS0S1S2S3S4S5S6S7S8S9S!S#S$S%S'S(S)S*S+S,S-S.S/S:S;S=S?S@S[S]S^S_S`S{S|S}S~SpmHeaTbTcTdTeTfT~ abgThTiTjTkTlTmTnToTpTqTBhrTsTtTuTvTwTxTyTzTATBTCTDTETFTGTHTITJTKTLTMTNTOTPTQTRTSTTTUTVTWTXTYTZT0T1T2T3T4T5T6T7T8T9T!T#T$T%T'T(T)T*T+T,T-T.T/T:T;T=T?T@T[T]T^T_T`T{T|T}T~TaUbUcUdUeUfUgUhUiUjUkUlUPEQERElqSEmUnUTEUE*u+uVEWEXEgnYEhnZEoU0EKe1E*h2EpU3E4Ejn5Ekn6E7EqU8E9E!E#Enq$ErUsU%E'E,u-u(E)E*Eon+Epn,EtU-EMe.E+h/EuU:E;Ern=Esn?E@E.u/u[E]Epg^Eqg_E`EPe{E,h|Erg}Esg~E:u;uRe=u?u]q^q@u[u]uHd^uId_uaF`ubFYb{u2c|ucF}uJd~uKdavbvcvdF. eF/ fF: gF; hF/hiFnbjFugkFvgdvwgevxglF:hmFtnnFunoF3cpFLdqFygrFpqsFvntFwnuFvFwFxFqqyFzFfvgvAFBFCFznDFAnEFvUFFwUUeGF;hHFxUIFCnJFDnKFLFMFNFEnOFyUPFQFhvivRFSFTFZjUF0jVFzUWFAUNdXFzgYFBUZF0F2j1F3j2F3F4Fjvkv5F6FWe7FXe8F9FYe!FAg#FZe$F0e%FlvmvnvGnov'Fpvqvrvsvtvuv9jvv!jwv(Fxv)FRdyvBgzv*FAv$jBv%jCvDvEv1eFv2eGv3eHv4eIvJv5eKv6eLv7eMv8eNv+FOvPv,F!e-F,i.FUd/FCg:F#e;F$e=F?F@Ftq[F]FQvRv^F_FKn`FLn{F|F'e}Fai~FaGMnbGNncGDgdGEgeGFgfGGggGOnhGPniGQnjGRnkGSnlGmGnGHgoGpGSvTvqGrGsG)etG*euGvG5cwG,exGyG-ezG.eAGBGUvVvCGDGicEGjcFGqbGGkcHGlcIGmcJGKGLGuqMGNGWvXvOGPGQGVnRGWnSGCUTG:eUGciVGDUWGYnXGZnYG5 ZG2bYv3bZvoc0G9c1G!c2G#c3G$c4G= 5G%c0v'c1vYd6G;e7G=e8GZd9G?e!G@e#G$G%Gdi'G(G2v3v)G*G+GLg,GMg-GEU.G0d/GNg:G;GOg=GPg?G@G[G]G4v5v^G_G5n`G6n{G|G`e}Ggi~G7naH8nbH6v7v8v]j9vcH!v#v_q`q$v%v'vji(vki)vdH*veH)c+v{e,vfH-vmi.vni/v9ngHhHiHjHzqkHFUGUlHmH:v;vnHoHpH$nqH%nrHHUsH}etHoiuHIUvHwH(nxH)nyHzH=v?vAHBHWgCHXgDHEHbfFHpiGHYgHHZgIH@v[vdf]v^v{q|q_v`v{v5d|v6d}vJH~vKH6baw,cbwLHcw7ddw8dewfwgwMH? NH@ OH[ PH] QHtiRHubSH0gTH1ghw2giw3gUHuiVH*nWH+nXH-cYH9dZH4g0HBq1H,n2H-n3H4H5H6HCq7H8Hjwkw9H!H#H:n$H;n%HJU'HKUgf(Hvi)HLU*H?n+H@n,H-H.H/HDq:HMU;H=Hlwmw?H@H[H^n]H_n^HNU_HOUif`Hwi{HPU|H}H{n~H|naIbIcInwowdIeIkffIlfgIhImfiI5gjInfkIoflIpwqwrw}nswmItwuwvwwwxwywqkzwrkAwnIBwoI%dCw6gDwpIEwtkFwukGwHwIwpfJwqfKwrfLwsfMwNwtfOwufPwvfQwwfRwqISwTwrIyfsIzftI)duI7gvIAfwIBfxIyIzIFqAIBIUwVwCIDIboEIcoFIGIDfHIEiIIJIdoKIeoLI8gMI9gNI!gOI#gPIfoQIgoRIhoSIioTIjoUIVIWI$gXIYIWwXwZI0I1IFf2IGf3I4I/c5IIf6I7IJf8IKf9I!IYwZw#I$Ixc%Iyc'Ixb(Izc)IAc*IBc+I,I-IGq.I/I0w1w:I;I=Imo?Ino@IQU[IMf]IGi^IRU_Ipo`Iqo{I6 |I9b2w!b3wDc}I?c~I@caJ[cbJ]ccJ^ dJ^c4w_c5w-deJNffJOfgJ.dhJPfiJQfjJkJlJFkmJnJ6w7woJpJqJIirJJisJSUtJSfuJKivJwJLixJMiyJzJAJBJ8w9wCJDJvoEJwoFJGJUfHJNiIJxoJJyoKJ!w#w$wMk%wLJ'w(w}q~q)w*w+wQi,wRi-wMJ.wNJ{c/wVf:wOJ;wTi=wUi?wAoPJTUUUVUWUQJRJSJMqTJXUYUUJVJ@w[wWJXJYJDoZJEo0JZU1JXf2JVi3J0U1U2U3U4U5U4J5JGo6JHo7J8J9J!JQq#J6U7U$J%J]w^w'J(J)JKo*JLo+J8U,JZf-JWi.J9U/J:JNo;JOo=J?J@J[JSq]J!U#U^J_J_w`w`J{J|JRo}JSo~J$UaK1fbKXicK%UdKeKUofKVogKhKiKjKUqkK'U(UlKmK{w|wnKoKpKYoqKcrrK)UsK3ftKYiuK*UvKwK0oxK1oyKzKAKBKWqCK+U,UDKEK}w~wFKGKHK4oIK5oJK-UKK5fLKZiMK.UNKOK7oPK8oQKRKSKTKYqUK/U:UVKWKaxbxXKYKZK!o0K#o1K;U2K7f3K0i4K=U5K6K%o7K'o8K9K!K#K0q$K?U@U%K'Kcxdx(K)K*K*o+K+o,K[U-K9f.K1i/K]U^U:K;K-o=K.o?K@K[K]K1q^K_U`U_K`Kexfx{K|K}K;o~K=oaL{UbL#fcL2idL|U}UeLfL@ogL[ohL~UaV5tbVcVdVeVfVgVhViVjVkVlVmVnVoVpVqVrVsVtVuVvVwVxVyVzVAVBVCVDVEVFVGVHVIVJVKVLVMVNVOVPV6t7t8t]oQVRVSVTVUVVVWVXVYVZV0V1V2V3V9t!t#t$t}X%t4V't(t)t*t+t5V6VKL7V8V9V!V#V$V%V'V(V)V*V+V,V-V.V/V:V;V=Vxr?V@V[V]V^V_V`V{V|V}V~VaWbWcWdWeWfWgWhWiWjWkWlWmWnWoWpWqWrWsWtWuWvWwWxWyWzWAWBWCWDWEWFWGWHWIWJWKWLWMWNWOWPWQWRWSWTWUWVWWWXWYWZW0W1W2W3W4W5W6W7W8W9W!W#W$W%W'W(W)W*W+W,W-W.W/W$f%f'f(f)f*f+f,f-f.f/f:f;f=f?f@f[f]f^f_f`f:W;W=W?W@W[W]W^W_W`W{W|W}W~WaXbXcXdXeXfXgXhXiXjXkXlXmXnXoXpXqXrXsXtXuX

102  

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

104 return cydriver._cuCtxGetDevice(device) 2a O1LbMbagS T .i7 2 * zbc d e f g h i j k l m n o p q r s t u v H I J K EAFA2qP1,rDuGAEuxl]iyl^izlAl3qhd~cadbd;d3 /bidjdAbBbCb#bDb8 9 ! + $b%b'bOc4q5q6q7q8q9q5i@kBlCl?b_i{d|d`iod}dChDhEhFhJlKl@b{i~dae|ipdbeGhHhIhJhRl}iSl~iTlUlVlajWlbjXlYlZl0l[bcjcededjqdeeKhLhMhNh7l8l]bejfegefjrdheOhPhQhRh(l)l^bgjiejehjsdkeShThUhVh:l;l_bijlemejjtdneWhXhYhZh_lkj`llj{l|l}lmj~lnjambmcmojdmpjemfm[k!q=dcdKPQ1LPMPNPOPEbFbGbHb:b;b(bxh?d/iNbOb@d:iL N #q|fX _ ` )b0 O M B C D b x , y z E | w F P Q R G Y Z Ib*b+bddQcU ?pFuR1@p[p^p_p`p$qhmqjnsimrjyrjmzrsjos{p|p}p~paqbqcqdqeq'itjgxhxixjxkxlxmxnx%qoxpxqxrxsxtxuxvxwxxxyxzx'q(qapAxBxKxLxMxNxOxPxHAIA/g:gLLQx|XJAKALAMANAOAPAQARAqsSATAUAVArsWAXAYAsstsZA0A1A2A3A4A5A6A7A8A9A!Aus#A$APP%A'A(A)A*A+A,A-AQP.A/A:A;A=A?A@A[A]A^A_A`A{A|ARP}A~AaBSPvsbBcBwsdBeBfBTPgBhBiBjBkBlBmBnBxsoBpBqBrBsBtBuBvBwBxByBzBABBBysCBDBEBFBGBzsHBIBAsJBKBLBMBNBOBPBQBRBSBTBUBVBBsUPWBXBYBCsZB0B1B2B3B4B5B6B7BDs8B9B!B#B$B%B'B(B)BEsBALzCADA~f1 RcMLlmNLalblcldlelfl{ glhliljlkl;iyhPcKb)i*i^dS1T1=i}g~gScahbhchdhehfhghhhihjhkhlhmhTcnhohphqhUcVcrhshthuhWcvhwhU1FsGsHsV1IsJsKsLsMsNsOsPsQsRsSsTsUsVsWsXsYsZs0s1s2s3s4s5s6s7s8s9s!s#s$s%s's|k_d{bomwXarbrCxxXyX(s)szXAX*s+s,sBX-sCX.sDXEX/s:s;sFX=sGXHX?s@sIXJXKXLXMXNXOXPX[s]sQX^sRX_s`sSXTXUX{s|sVXWXXXYXZX}s0X1X2X3X4X5X~s6X7Xat8X9X!X#Xbt$Xct%X'X(X)X*Xdt+Xet,Xftgt-X.Xht/Xit:Xjt;Xkt=Xlt?Xmt@X[X]X^X_Xnt`Xot}k#i$iUbW1]kXcGu^kHu1h2h3hIukb%ivd_kX14hvewd|b5hweCjxe6hye7hzexd}b8hAegg*Byd+Bhg,Big-Bjg.Bkg/BYc:Blg;B9hBezd~b!hCeDjDe#hEe$hFeAdac%hGemgng'hBdZcCdILGxpmfp=gHe`kVbbcIekq(h)hVPedfd~ abgd=BJuqm~Xrm)qsm*qtmaYumbYvm4 wmBh+q,q-q.q/q:q;q=q?q@qHxxmymptqtrtstttut?Bzm@BAm[BBm]BCm^BDm_BEmKuFmLuGmMuHmNuImOuJmPuKmQuLmRuMmSuNmTuOmUuPmVuQmWuRmXuSmYuTmZuUm0uVm1uWmY1XmZ1Ym`BZm{B0m|B1m}B2m~B3maC4mbC5mcC6mdC7meC8mfC9mgC!mhC#miC$mjC%mkC'mlC(mmC)mnC*moC+mpC,m01-mcY.mdY[qeY/mfY:mgY;mhY=miY?mjY@mkY[mlY]mmY^mnY_moY`mpY{mqY|mrY}m~menccGjJjinJeKe*hmqlnmndcMjPjqnLeMe+hoqWbNeOeQjogpgqgDdPe,hrgsgQe( EdFdSeXbYb2ctglbmbZb. / : ; /hnbugxg3cLdygxnecTjWjBnTeUe;hrqXj0b?h]h1jMdNdzgFn4jobOdPd^hVeWeXe4cYeAgZe0e5j1b`h{h#jQdRdBgHnpbSdTd9e!e,iUdCg#e$eInfc'j*j%e'eaibigcHgIgVdWdJg+j(e)e*e+e5c,e,j-e.ehc6c7c8cXdicjcqbkclcmcTnnc-j:jXn/e:ecivq5 2b3boc9c!c#c$c= %c'cYd;e=eZd?e@e;jpcdiei[e]efi0nKgLgMg1n^e0dNg2nOgPg3nqc=j[j_e`egihirbRgUgli(c)c{e^j!nrc`j}j'n|e}eoiAq4b~eaf~jVgWgXg1dbfpiYgZgcf) 2d3def5b6b,crisbtb7b? @ [ ] tiub0g3g-c9d4g.nscckfk=nffgfviHt[ntchkkk`nhfifwiItlkvb!d#dxijfkflf.cmf5gnfofmk8bziAisk$d%d6gEqwb'd(dxfyfzf)d7gAfBf~nucvkykCfDfEiFivc$g%g*d+d'gzkEfFfGfHf/cIfAkJfKfwc:c;c=c,dxcycxbzcAcBckoCcBkEkooLfMfGiMt6 9b!bDc?c@c[c]c^ ^c_c-dNfOf.dPfQfroEcFkGk(g)gHkHqHiIiJisoRfSfKiIqLiMitoFcIkLkTfUfNiOiyb+g.gSi`c{cVfzoPtQtBoGcOkRkFoWfXfViNqOqPqRtStTtIoHcTkWkMoYfZfWiRqPoIcYk1kTo0f1fXiTqWoJc3k6kZo2f3fYiVq2oKc8k#k6o4f5fZiXq9oLc%k)k$o6f7f0iZq(oMc+k.k,o8f9f1i0t1t/oNc:k?k?o!f#f2i2t3tWPXP5tYPZP11216t7t8t]o9t!t#t$t}X%t2u't(t)t*t+t31KL3u{X41RxSxTxUxVxWxxrXxYxZx0x1x2x3x4x5xll6xerAr7xzh8x,t-t.t/t:t;t=t?t@t[t]t^t_t`t{t|t}t~taubucudueufuguhuiujukulumunuoupuqurusutuuuvuwu5161718191!1#1$1%1'1(1)1*1+1,1-1.1/1:1;1=1?1@1[1$f%ffrgrhr'f(f)firjrkrlrmrnr*f+f,f-f.forprqr/f:f;f=f?f@f[frrsrtr]f^furvr_fwr`f]1^1

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) 2LbMbagS T .i7 2 * zbc d e f g h i j k l m n o p q r s t u v H I J K hd~cadbd;d3 /bidjdAbBbCb#bDb8 9 ! + $b%b'bOccd:b;bNbObL N X _ ` 0 O M B C D b ,b-b.bkdldmdx , y z E | w F P Q R PbQbRb# $ % G Y Z Ib*b+bddQcU bg`dmlnlndolplyrzrcgdgkplpmpnpop'i' A `oqe{o|o}o3i~o`bqlOLPLSb4ibbcb- {fTbdbebfbgbhbibjbKxLxMxNxOxPxQx~f1 Rcalblcldlelfl{ glhliljlkl;iyhPc?gdp@g[gep]g^g_g(i`g{g|g{k9xJbV W sYQL?iKb)i*i^d=i_d{bBrCrppDrqpErFrrpspGrHrIrtpJrupvpwpxpypzpApBpCpKrDpEpFpGpLrHpIpMrNrOrPrJpQrKpRrSrLpMpTrUrVrNpWrOpPpQpRpSpTpUpVpWpXrXpYpZp0pYr1p2pZr0r1r2r3p3r4p4r5r5p6p6r7r8r7p9r8p9p!p#p$p%p'p(p)p!r*p+p,p-p#r.p/p$r%rUbkbfpVb4 +iwtxtytsqhiQgrb]jEtRgwqSgTgUgxqiijikili(cFt)c{e^jyqminiGtJtOi*gybMkNt+gJq,g-g.gKqPiQiRiSi`cOt{cVfzoLqTiUi/d:dUtVtWtXtYtZtJL4tRxSxTxUxVxWxxrXxYxZx0x1x2x3x4x5xll6xerAr7xzh8x

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]d6i7i8i}f9i!i

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_1

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]d6i7i8i}f9i!i

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]d6i7i8i}f9i!i

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) 2S T 7 2 * zbc d e f g h i j k l m n o p q r s t u v H I J K 3 AbBbCb#bDb5i@k?bod@bpd[bqd]brd^bsd_btd=dEbFbGbHb(bL N #q|fX _ ` )bO M B C D b x , y z E | w F P Q R G Y Z Ib*b+bddQcU ' A 1 { PcuemmnmKb^d=i}g~gScahbhchdhehfhghhhihjhkhlhmhTcnhohphqhUcVcrhshthuhWcvhwhJuqmrm)qsm*qtmumvm4 wmBh+q,q-q.q/q:q;q=q?q@qHxxmtYymuY`1vYzmAmBmCmDmEmFmGmHmImJmKmLmMmNmOmPmQmRmSmTmUmVmWmXmYmZm0m1m2m3m4m5m6m7m8m9m!m#m$m%m'm(m)m*m+m,m-m.m[q/m:m;m=m?m@m[m]m^m_m`m{m|m}m~mccinJemqlndcqnLeoqWbDd( SeXbtglbmbZb. / : ; nb3cecBnTerq0b1jMdFnob4c1b#jQdHnpbfc%ebigcHgIgVdWdJg+j(e)e*e+e5c,e,j-e.ehc6c7c8cXdicjcqbkclcmcncXn/evq5 = ;jpcdiei[e]efi0nKgLgMg1n^e0dNg2nOgPgqc_erbli(c^jrc'n|eAq4b1d) ef5bsbtb7b? @ [ ] ub-csc=nfftc`nhfvb.c8bsk$dwbucCfFivc$g%g*d+d'gzkEfFfGfHf/cIfAkJfKfwc:c;c=c,dxcycxbzcAcBcCcooLf6 ^ EcsoRfFcTfybSi`cGcFoWfNqOqPqHcMoYfRqIcTo0fTqJcZo2fVqKc6o4fXqLc$o6fZqMc,o8fNc?o!f]o2u3u

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) 2wYxYyY

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) 2S T 7 2 * zbc d e f g h i j k l m n o p q r s t u v H I J K 3 AbBbCb#bDb5i@k?bod@bpd[bqd]brd^bsd_btd=dEbFbGbHb(bL N #q|fX _ ` )bO M B C D b x , y z E | w F P Q R G Y Z Ib*b+bddQcU ' A 1 { PcuemmnmKb^d=i}g~gScahbhchdhehfhghhhihjhkhlhmhTcnhohphqhUcVcrhshthuhWcvhwhJuqmrm)qsm*qtmumvm4 wmBh+q,q-q.q/q:q;q=q?q@qHxwYxmtYymxYuYyYvYzmAmBmCmDmEmFmGmHmImJmKmLmMmNmOmPmQmRmSmTmUmVmWmXmYmZm0m1m2m3m4m5m6m7m8m9m!m#m$m%m'm(m)m*m+m,m-m.m[q/m:m;m=m?m@m[m]m^m_m`m{m|m}m~mccinJelndcqnLeWbDd( SeXblbmbZb. / : ; nb3cecBnTe0b1jMdob4c1b#jQdpbfc%ebigcHgIgVdWdJg+j(e)e*e+e5c,e,j-e.ehc6c7c8cXdicjcqbkclcmcncXn/e5 = pc1n^eqc_erbli(crc'n|e4b1d) ef5bsbtb7b? @ [ ] ub-csc=nfftc`nhfvb.c8bsk$dwbucCfFivc$g%g*d+d'gzkEfFfGfHf/cIfAkJfKfwc:c;c=c,dxcycxbzcAcBcCcooLf6 ^ EcsoRfFcTfybSi`cGcFoWfHcMoYfIcTo0fJcZo2fKc6o4fLc$o6fMc,o8fNc?o!f]o2u3u

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) 2#q|fX ~X)q*qaYbYKuLuMuNuOuPuQuRuSuTuUuVuWuXuYuZu0u1ucYdYeYfYgYhYiYjYkYlYmYnYoYpYqYrY

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{1

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) 24 Bh+q,q-q.q/q:q;q=q?q@q|1

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'i!xzY} AYBYCYDYEYFYGYHYIYJYKY[d]d|k_d{bomCxBrCrppDrqpErFrrpspGrHrIrtpJrupvpwpxpypzpApBpCpKrDpEpFpGpLrHpIpMrNr}kGxpmfp

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) 20 x , y z E | w F P Q R uEvEwExE$qyEAECE'rEEFE'iA `budreSbbbcb- Tbdbseteebfbgbhbibjbbp!x(rzY} AYBYCYDYEYFYGYHYIYJYKb)i*iKY[d]d|k_d{bombrCxhqDxBrCrppDrqpErFrrpspGrHrIrtpJrupvpwpxpypzpApBpCpKrDpEpFpGpLrHpIpMrNr1r2r3p3r4p4r5r5p6p6r7r8r7p9r8p9p!p#p$p%p'p(p)p!r*p+p,p-p#r.p/p$r%r}k]kGxpmfp

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) 2S 2 c d e f g h i j k l m n o p q r s t u v H I J K O M B C D b =bG Y Z ' A 1 { JbV W Kb}g~gScahbhchdhehfhghhhihjhkhlhmhTcnhohphqhUcVcrhshthuhWcvhwh|k_d{barExiqOrPrJpQrKpRrSrLpMpTrUrVrNpWrOpPpQpRpSpTpUpVpWpXrXpYpZp0pYr1p2pZr0r}k4

288  

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

290 return cydriver._cuMemFreeHost(p) 2S 2 c d e f g h i j k l m n o p q r s t u v H I J K O M B C D b =bG Y Z A LYMY1 { JbV W Kb}g~gScahbhchdhehfhghhhihjhkhlhmhTcnhohphqhUcVcrhshthuhWcvhwh|k_d{barExiqOrPrJpQrKpRrSrLpMpTrUrVrNpWrOpPpQpRpSpTpUpVpWpXrXpYpZp0pYr1p2pZr0r}k4

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) 2LYMY

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) 2x , y z E | w F P Q R @p[p^p_p$qhmimjm'r{p|p' A Sb4ibbcb- {fTbdbebfbgbhbibjbbp(rKb)i*i|k_d{bbrhqDx1r2r3p3r4p4r5r5p6p6r7r8r7p9r8p9p!p#p$p%p'p(p)p!r*p+p,p-p#r.p/p$r%r}k]k

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) 2' A `oqe{o|o}o3i~o`bql+i/d:d

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) 2jqFx

333  

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

335 return cydriver._cuMemHostUnregister(p) 2jqFx

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!x}

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) 28 9 ! + L N !x}

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) 2x , y z E | w F P Q R ' A Sb4ibbcb- {fTbdbebfbgbhbibjbJbV W Kb)i*i_d{bUbkbVb4

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) 2L N x , y z ppspupvpwpDpEpJpMpOpPpQpXpYp3p6p8p9p!p*p+p

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) 2qpxpypzpFpGpKpRpSpTpZp0p4p#p$p%p,p-p

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) 2rptpApBpCpHpIpLpNpUpVpWp1p2p5p7p'p(p)p.p/p

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) 2NY

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) 2NY

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) 2edfd~ abgd

504  

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

506 return cydriver._cuMemAddressFree(ptr, size) 2edfd~ abgd

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) 2edfd~ abgd

510  

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

512 return cydriver._cuMemRelease(handle) 2edfd~ abgd

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) 2edfd~ abgd

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) 2edfd~ abgd

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) 2edfd~ abgd

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) 2edfd~ abgd

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) 2edfd~ abgd

543  

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

545 return cydriver._cuMemFreeAsync(dptr, hStream) 2L 0 ,b-b.bkdldmdx , y z E | w F P Q R PbQbRb# $ % bg`dRLzEndBEDEcgdgkplpmpnpopoepeA qe`begud#x$x%x'x(x)x*x+x,x-x.x/xreSbbbcb- Tbdbse0hteebfbgbhbibjb/g:gJbV W ;gfg#i$iUbXc^kkb%ivd_kwd|bxd}bydYczd~bAdacBdZcCdEj=gHe`kVbbcIe4 QE7E!E:u;u=u?u]q^q@u[u]u^u_uaF`ubF{u|ucF}u~uavwFMFmv7viH@v[v]v^v{q|q_v`v{v|v}vJH~vKHawbwLHcwdwew5H.Hqw#w|c}cRJ9J@JiKAKSK!K[K$f%ffrgrhr'f(f)firjrkrlrmrnr*f+f,f-f.forprqr/f:f;f=f?f@f[frrsrtr]f^furvr_fwr`fcp

546  

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

548 return cydriver._cuMemAllocAsync(dptr, bytesize, hStream) 2kdldmdx y z E w F P Q R PbQbRb# $ %

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:x;g

555  

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

557 return cydriver._cuMemPoolGetAttribute(pool, attr, value) 2L N ,b-b.bx , y z E | w F :x/g:gJbV W ;gfg#i$i%i4hvewd|b5hweCjxe6hye7hzexd}b8hAeggydhgigjgkgYclg9hBezd~b!hCeDjDe#hEe$hFeAdac%hGemgng'hBdZcCd=g4 FjKjLjQe( ReEd0c1cFd-hGdHdIdSeXbRjYb2ctg.hJdKdSj=h_hQg_jcf) df2d*c+c3dqi4d5d6def5bak6b,crisi7d8dbkgkyi*gNkSkXk2k7k$k*k/k$f%f'f(f)f*f+f,f-f.f/f:f;f=f?f@f[f]f^f_f`fcp

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) 20 dzezfzgzhzizoejzpekzA qe`begudlzmznzozpzqzrzsztzuzvzwzxzyzzzAzBzCzDzEzFzGzHzIzJzKzreSbbbcb- Tbdbse0hteebfbgbhbibjbUbXc1h2h3hkbvd4hvewd|b5hweCjxe6hye7hzexd}b8hAeggydhgigjgkgYclg9hBezd~b!hCeDjDe#hEe$hFeAdac%hGemgng'hBdZcCdEjVbbcIekq(h)hanbncndn|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) 2iLtj^ojL_ogxkLhxoelLpeixmLjxnLkxoLlxpLqLrLsLtLuLkmvLwLxLyLzLmxnx%qoxpxqxrxsxtxuxvxwxALxxBLyxCLzxDL'qEL(q- {fFLapGLAxHLBxebfbgbhbibjb:xUbXc1h2h3hkbvd4hvewd|b5hweCjxe6hye7hzexd}b8hAeggydhgigjgkgYclg9hBezd~b!hCeDjDe#hEe$hFeAdac%hGemgng'hBdZcCdEjVbbcIekq(h)hanbncndn|c}c

567  

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

569 return cydriver._cuMemPoolDestroy(pool) 20 dzezfzgzhzizoejzpekzA qe`begudlzmznzozpzqzrzsztzuzvzwzxzyzzzAzBzCzDzEzFzGzHzIzJzKzreSbbbcb- Tbdbse0hteebfbgbhbibjb:xUbXc1h2h3hkbvd4hvewd|b5hweCjxe6hye7hzexd}b8hAeggydhgigjgkgYclg9hBezd~b!hCeDjDe#hEe$hFeAdac%hGemgng'hBdZcCdEjVbbcIekq(h)hanbncndn|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) 2?pFu`phmqjndimrjjmsj}p~paqbqcqdqeq]kXcGu^kHu1h2h3hIukbvd_kgg*Byd+Bhg,Big-Bjg.Bkg/BYc:Blg;BngZcHe`k

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) 2L N ,b-b.bx , y z E | w F bg`dRLqjndrjsjcgdgkplpmpnpop^o_ofqxuoepe' A egud#x$x%x'x(x)x*x+x,x-x.x/xgqyuzuAureBuSb4ibbcb- {fTbdbse0hteCuebfbgbhbibjb/g:gJbV W ;gfg#i$iUbXc^kkb%ivd_kwd|bxd}bydYczd~bAdacBdZcCdEj=gHe`kVbbcIe4 FjKjLjQe( ReEd0c1cFd-hGdHdIdSeXbRjYb2ctg.hJdKdSj=h_hQg_jcf) df2d*c+c3dqi4d5d6def5bak6b,crisi7d8dbkgkyi*g|c}cNkSkXk2k7k$k*k/k$f%ffrgrhr'f(f)firjrkrlrmrnr*f+f,f-f.forprqr/f:f;f=f?f@f[frrsrtr]f^furvr_fwr`fcp

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) 2iLtj^ojL_ogxkLhxoelLpeixmLjxnLkxoLlxpLqLrLsLtLuLkmvLwLxLyLzLmxnx%qoxpxqxrxsxtxuxvxwxALxxBLyxCLzxDL'qEL(q- {fFLapGLAxHLBxebfbgbhbibjbve|bwexeyeze}bAeBe~bCeDeEeFeacGebc(h)hanbncndn|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) 2^o_ofqxuoepe' A egud#x$x%x'x(x)x*x+x,x-x.x/xgqyuzuAureBuSb4ibbcb- {fTbdbse0hteCuebfbgbhbibjbbc|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) 28 9 ! + }dbeeehekene(rKeMePeYbLdUeNdYeRdUd'e5cqb:e5 2b3boc9c!c#c$cZd0d`e)c}ebf6b9dgfifmf%d)dDf/cxbMf6 9b!bDc?c@c[c]c.dSfUf{cXfZf1f3f5f7f9f#f

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) 2mlnlndolpl

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) 2msgm]pOY'rSLTLbp

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) 2bg`dcgdg

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) 2bgmlnl

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) 2`dnd

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) 2`dmsgm]pndolpl'rSLTLcgdgbp

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) 2bp

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) 2(r

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) 2S 2 c d e f g h i j k l m n o p q r s t u v H I J K O M B C D b =bG Y Z bg`dmsgm]pOYmlnlndolplyrzr'rSLTLcgdg'i(r}1JbV W }g~gScahbhchdhehfhghhhihjhkhlhmhTcnhohphqhUcVcrhshthuhWcvhwharbr;gfg~1hqDxExiqjqFx]kXc=gHe4 a2b2c2d2e2f2g2h2i2

648  

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

650 return cydriver._cuStreamCreate(phStream, Flags) 2@iULAh} PY[d]d6i7i8i}f9i!i

651  

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

653 return cydriver._cuStreamCreateWithPriority(phStream, flags, priority) 2LbMbagS T .i7 2 * zbc d e f g h i j k l m n o p q r s t u v H I J K hd~cadbd;d3 /bidjdAbBbCb#bDb8 9 ! + $b%b'bOccd:b;bNbObL N X _ ` 0 O M B C D b ,b-b.bkdldmdx , y z E | w F P Q R PbQbRb# $ % G Y Z Ib*b+bddQcU bg`dmlnlndolplyrzrcgdgkplpmpnpop'i' A `oqe{o|o}o3i~o`bqlOLPLSb4ibbcb- {fTbdbebfbgbhbibjbKxLxMxNxOxPxQx~f1 Rcalblcldlelfl{ glhliljlkl;iyhPc?gdp@g[gep]g^g_g(i`g{g|g{kKb)i*i^d=i_d{bBrCrppDrqpErFrrpspGrHrIrtpJrupvpwpxpypzpApBpCpKrDpEpFpGpLrHpIpMrNrOrPrJpQrKpRrSrLpMpTrUrVrNpWrOpPpQpRpSpTpUpVpWpXrXpYpZp0pYr1p2pZr0r1r2r3p3r4p4r5r5p6p6r7r8r7p9r8p9p!p#p$p%p'p(p)p!r*p+p,p-p#r.p/p$r%rUbkbfpVb4 +iwtxtytsqhiQgrb]jEtRgwqSgTgUgxqiijikili(cFt)c{e^jyqminiGtJtOi*gybMkNt+gJq,g-g.gKqPiQiRiSi`cOt{cVfzoLqTiUi/d:dUtVtWtXtYtZtJL4tRxSxTxUxVxWxxrXxYxZx0x1x2x3x4x5xll6xerAr7xzh8x

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) 

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) 2T 7 c d e f g h i j k l m n o p q r s t u v U zh

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) 2LbMbagS T .i7 2 * zbc d e f g h i j k l m n o p q r s t u v H I J K ,b-b.bkdldmdx y z E w F P Q R PbQbRb# $ % G Y Ib*b+bddQcU

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) 1cdefghijklmnopqrstuvHIJKGU

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) 2LbMbagS T .i7 2 * zbc d e f g h i j k l m n o p q r s t u v H I J K ,b-b.bkdldmdx y z E w F P Q R PbQbRb# $ % G Y Ib*b+bddQcU

696  

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

698 return cydriver._cuStreamIsCapturing(hStream, captureStatus) 2L N ,b-b.bkdldmdx , y z E | w F P Q R PbQbRb# $ % bg`dRLqjndrjsjcgdgkplpmpnpop^o_ofqxuoepe' A egud#x$x%x'x(x)x*x+x,x-x.x/xgqyuzuAureBuSb4ibbcb- {fTbdbse0hteCuebfbgbhbibjb/g:gJbV W ;gfg#i$iUbXc^kkb%ivd_kwd|bxd}bydYczd~bAdacBdZcCdEj=gHe`kVbbcIe4 FjKjLjQe( ReEd0c1cFd-hGdHdIdSeXbRjYb2ctg.hJdKdSj=h_hQg_jcf) df2d*c+c3dqi4d5d6def5bak6b,crisi7d8dbkgkyi*g|c}cNkSkXk2k7k$k*k/k$f%ffrgrhr'f(f)firjrkrlrmrnr*f+f,f-f.forprqr/f:f;f=f?f@f[frrsrtr]f^furvr_fwr`fcp

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) 2LbMbagS T .i7 2 * zbc d e f g h i j k l m n o p q r s t u v H I J K ,b-b.bkdldmdx y z E w F P Q R PbQbRb# $ % G Y Ib*b+bddQcU

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) 1ScdefghijklmnopqrstuvHIJKGU

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) 2LbMbS T 2 * zbc d e f g h i j k l m n o p q r s t u v H I J K hd~cadbd;d3 /bidjdAbBbCb#bDb8 9 ! + $b%b'bOccd:b;bNbObL N X _ ` 0 O M B C D b =bx , y z E | w F P Q R PbQbRb# $ % G Y Z bg`dmlnlndolplcgdgA } ~f1 Rc{ JbV W ?iKb[d]d6i7i8i}f9i!i^d=i}g~gScahbhchdhehfhghhhihjhkhlhmhTcnhohphqhUcVcrhshthuhWcvhwh4 Arzh

714  

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

716 return cydriver._cuStreamDestroy_v2(hStream) 2LbMbagS T .i7 2 * zbc d e f g h i j k l m n o p q r s t u v H I J K hd~cadbd;d3 /bidjdAbBbCb#bDb8 9 ! + $b%b'bOccd:b;bNbObL N X _ ` 0 O M B C D b ,b-b.bkdldmdx , y z E | w F P Q R PbQbRb# $ % G Y Z Ib*b+bddQcU bg`dmlnlndolplyrzrcgdgkplpmpnpop'iA 3i`bqlOLPLudreSbbbcb- TbdbseteebfbgbhbibjbKxLxMxNxOxPx@iULAh} Qx~f1 Rcalblcldlelfl{ glhliljlkl;iyhPc?g@g[gep]g^g_g`g{g|g;x9xJbV W QL?iKb)i*iPY[d]d6i7i8i}f9i!i^d=i_d{bBrCrppDrqpErFrrpspGrHrIrtpJrupvpwpxpypzpApBpCpKrDpEpFpGpLrHpIpMrNrOrPrJpQrKpRrSrLpMpTrUrVrNpWrOpPpQpRpSpTpUpVpWpXrXpYpZp0pYr1p2pZr0r1r2r3p3r4p4r5r5p6p6r7r8r7p9r8p9p!p#p$p%p'p(p)p!r*p+p,p-p#r.p/p$r%rUbkbILVb4 +i4E8E;E0F6v7v8v9vcH!v#v_q`q$v%v'v(v)vdH*veH+v,vfH-v.v/vwH}H!w#w$w%wLJ'w(w}q~q)w*w+w,w-wMJ.wNJ/w:wOJ;w=w?w/d:d5J:JeKwKOK6K;KfLRxSxTxUxVxWxxrXxYxZx0x1x2x3x4x5xll6xerAr7xzh8x

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) 2T 7 c d e f g h i j k l m n o p q r s t u v /b{d|d~daecedefegeiejelemexh?d/iNbOb@d:iX U ' A `oqe{o|o}o3i~o`bqlLL~f1 RcMLlmNLalblcldlelfl{ glhliljlkl;iyhPc?iQY+i6zHjIj!zNjOjNeOe0c1clbmbvgwgUjVjzt@h[hOdPd5j_h1bGn*z`h6j7j{hCt8j9j!j#jQd+zRdBgHnDt$j%j|h}h1e2e3e4e~h5e6e7e8eSdTd(j)jVdWd6c7c.j/j2b3b%c'c[e]e?j@jwqSgTg/z{j|j~eaf*c+csbtb1g2gdkek@zikjk!d#dmkyi8b}n^zzinkokAiKtpkqkrksk$d_z%d6gEqLttkukBiCipfqfrfsfDitfufvfwf'd(dwkxk*d+d:c;cCkDk9b!b^c_c(g)gJkKkJq,g-g/d:d~zPkQkcAUkVkgAZk0kkA4k5koA9k!ksA'k(kvA,k-kyA;k=kllzh

729  

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

731 return cydriver._cuEventRecord(hEvent, hStream) 2T 7 c d e f g h i j k l m n o p q r s t u v U ' A `oqe{o|o}o3i~o`bql~f1 Rcalblcldlelfl{ glhliljlkl;iyhPc?i+i/d:dllzh

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) 2xh?d@d{ ;iyh

738  

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

740 return cydriver._cuEventSynchronize(hEvent) 21 { yhPc?i

741  

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

743 return cydriver._cuEventDestroy_v2(hEvent) 2T 7 c d e f g h i j k l m n o p q r s t u v 4u5u6u7u8u9u!u#u$u%u'u(u)uxh?d/i@d:iU A 3i`bqlLL~f1 RcMLlmNLalblcldlelfl{ glhliljlkl;iyhPc?iQY+iUE*u+u'E,u-u.u/u]q^qbvcvdvevfvgvQFhvivjvkvlvmvnvov'Fpvqvrvsvtvuvvvwv(Fxv)Fyvzv*FAvBvCvDvEvFvGvHvIvJvKvLvMvNvOvPvQvRvSvTvUvVvWvXvYvZv0v1v2v3v4v5v#v_q`qmH:v;v=v?v{q|qfwgwhwiwjwkw=HlwmwnwowpwqwrwswmItwuwvwwwxwywzwAwnIBwoICwDwpIEwFwGwHwIwJwKwLwMwNwOwPwQwRwSwTwUwVwWwXwYwZw0w1w2w3w4w5w6w7w8w9w(w}q~q/d:dVJ@w[w%J]w^w_J_w`wmK{w|wEK}w~wWKaxbx'Kcxdx`Kexfxllzh

744  

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

746 return cydriver._cuEventElapsedTime_v2(pMilliseconds, hStart, hEnd) 2~f1 RcPc

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) 2j2

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]d6i7i8i}f9i!i

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) 2S T 7 2 * zbc d e f g h i j k l m n o p q r s t u v H I J K x , y z E | w F P Q R G Y Ib*b+bddQcU ' A 1 { PcJbV W Kb^d=i}g~gScahbhchdhehfhghhhihjhkhlhmhTcnhohphqhUcVcrhshthuhWcvhwh4

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) 2LbMb

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) 2PyQyRySyTyUyVyWyXyxl]iylYy^izlAlZy0y1yvX2y[i3y4y5y6y3 7y8y9y!y#y$y%y'y(y)y*y+y,y-y.y/y:y;y=y?y@y[y]y^y_y`y{y|y}y~yazBlCl?b_i{d|d`iDlElFlGlod}dChDhEhFhHlIlJlKl@b{i~dae|iLlMlNlOlpdbeGhHhIhJhPlQlRl}iSlbz~iTlUlVlajWlbjXlYlZl0l[bcjcededj1l2l3l4lqdeeKhLhMhNh5l6l7l8l]bejfegefj9l!l#l$lrdheOhPhQhRh%l'l(l)l^bgjiejehj*l+l,l-lsdkeShThUhVh.l/l:l;l_bijlemejj=l?l@l[ltdneWhXhYhZh]l^l_lkj`llj{l|l}lmj~lnjambm=xcmojdmpjemfmtlRYSYTYUYJxVY?x-r[k!q=dulcdgphpipjpEbFbGbHb:b;b(bxh?d/iNbOb@d:iL N |fX _ ` )b0 -iO M B C D VL:prlslb vl=bwlZ WL@i)rXL*r+r@x[xAh} ]xYLWYencclqGjHjIjJj7zfngnhnJeKe*h8zjnknmndcnqMjNjOjPj#znnonpnLeMe+h$zrnsnWbNeOeQjogpgqgDdPe,hrgsgQe( ReEd0c1cFd-hGdHdIdXbYb2c.hJdKdlbmbZb. / : ; /hnbugvgwgxg:htnun3cLdygpqvnwnxnecqqTjUjVjWj%zynznAnTeUe;h'zCnDnXj0bEn?h@h[h]hAtYjZj0jMdNdzgBt2j3j4jobOdPd^hVeWeXe4cYeAgZe0e5j1bGn`h6j7j{hCt8j9j!jQdRdBgDt$j%j|h}h1e2e3e4e~h5e6e7e8epbSdTd9e!e,iUdCg#e$eInfctq'j(j)j*jJnKnLn%e'eai,zMnNnDgEgFgGgOnPnQnRnSnbigcHgIgVdWdJg+j(e)e*e+e5c,e,j-e.ehc6c7c8cXdicjcqbkclcmcTnncuq-j.j/j:j-zUnVnWn/e:eci.zYnZn5 2b3boc9c!c#c$c= %c'cYd;e=eZd?e@e;jpcdiei[e]efi0nKgLgMg^e0dNg2nOgPg3nqc=j?j@j[j4n5n6n_e`egi7n8nhirb]jRgSgTgUgxqiijiki(c)c{eyqmini9n!nrczq`j{j|j}j:z#n$n%n|e}eoi;z(n)n4b~eaf~jVgWgXg1dbfpiYgZgcf) df2d*c+c3dqi4d5d6d5b6b,csi7d8dsbtb7b? @ [ ] tiub0g1g2g3gui*n+n-c9d4gBq,n-n.nscCqckdkekfk=z/n:n;nffgfvi?z?n@n[ntcDqhkikjkkk[z]n^n_nhfifwi]z{n|nlkvb!d#dxijfkflf.cmf5gnfofmk8b}nzinkokAiKtpkqkrk$d%d6gLttkukBiCipfqfrfsfDitfufvfwfwb'd(dxfyfzf)d7gAfBf~nucFqvkwkxkykaobocoCfDfEi`zdoeo8g9g!g#gfogohoiojoFivc$g%g*d+d'gzkEfFfGfHf/cIfAkJfKfwc:c;c=c,dxcycxbzcAcBckoCcGqBkCkDkEk{zlomonoLfMfGi|zpoqo6 9b!bDc?c@c[c]c^ ^c_c-dNfOf.dPfQfroEcFkGk(g)gHkHqHiIiJiRfSfKiIqLiMitoFcIkJkKkLkuovowoTfUfNixoyoOiybMk+g,g-g.gKqPiQiRi`c{cVfLqTiUiAoBoGcMqOkPkQkRkaACoDoEoWfXfVibAGoHoIoHcQqTkUkVkWkdAJoKoLoYfZfWieANoOoPoIcSqYkZk0k1khAQoRoSo0f1fXiiAUoVoWoJcUq3k4k5k6klAXoYocr2f3fYimA0o1o2oKcWq8k9k!k#kpA3o4o5o4f5fZiqA7o8o9oLcYq%k'k(k)ktAdr!o#o6f7f0iuA%o'o(oMc0q+k,k-k.kwA)o*o+o8f9f1ixA-o.o/oNc1q:k;k=k?kzA:o;o=o!f#f2iAA@o[o

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) 23 AbBbCb#bDb5i@k?bod@bpd[bqd]brd^bsd_btd=dEbFbGbHb(bL N |fX _ ` )bO M B C D b Z ccJedcLeWbDd( XblbmbZb. / : ; nb3cecTe0bMdob4c1bQdpbfc%egc+ehc6c7c8cXdicjcqbkclcmcnc/e5 = pc^eqc_erb(crc|e4b1d) 5bsbtb7b? @ [ ] ub-cscfftchfvb.c8b$dwbucCfvcHfwc:c;c=c,dxcycxbzcAcBcCcLf6 ^ EcRfFcTfyb`cGcWfHcYfIc0fJc2fKc4fLc6fMc8fNc!f

870  

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

872 return cydriver._cuGraphKernelNodeGetParams_v2(hNode, nodeParams) 2ZLEbFbGbHb(b)bb

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) 28 9 ! + }dbeeehekeneKeMePeYbLdUeNdYeRdUd'e5cqb:e5 2b3boc9c!c#c$cZd0d`e)c}ebf6b9dgfifmf%d)dDf/cxbMf6 9b!bDc?c@c[c]c.dSfUf{cXfZf1f3f5f7f9f#f

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) 28 9 ! + $b%b'bOcChDhEhFhGhHhIhJhKhLhMhNhOhPhQhRhShThUhVhWhXhYhZhb =b*h+h,h2cyg;hzgAgBgCgai,ekcci= %c'cYd;e=eZd?e@eNggi{eoipi,c4gviwi5g6g7gEiIfzcGi^ ^c_c-dNfOf.dPfQfKiNiVfViWiXiYiZi0i1i2i

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) 2hdidjdDlElLlMl1l2l9l!l*l+l=l?l:b;b0 fnnnogGdZb:hynYjVe8j}h~h9eJnDgEgFgGg(eXdUnocYdKg4nii#nVg4d7bui/n]njfpkCiDixfao8g9g!g#gEf,dloDc-dHiuoPiCoJoQoXo3odr)o:o

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) 2S 3 ?b@b[b]b^b_b(b)bccdcWb( lbmbZb. / : ; nbec0bob1bpbfcgchcnc5 = pcqcrbrc4b) sbtb7b? @ [ ] ubsctcvb8bwbucvcwcCc6 ^ EcFcybGcHcIcJcKcLcMcNc

906  

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

908 return cydriver._cuGraphChildGraphNodeGetGraph(hNode, phGraph) 23 ?b@b[b]b^b_b(b)bccdcWb( lbmbZb. / : ; nbec0bob1bpbfcgchcnc5 = pcqcrbrc4b) sbtb7b? @ [ ] ubsctcvb8bwbucvcwcCc6 ^ EcFcybGcHcIcJcKcLcMcNc

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^i[i8 9 ! + 7q8q9q_i}d{ibe}i~iajbjcjeeejhegjkeijnekjljmjnj=xojpj?x[kO M B C D VL:prlslvlwl@i)r*r+r@x[x]xYLGjKeMjMePeEdYbugLdTjUe?hNd4jobOdPd^hVeWeXe4cYeAgZe0e`hRdUd'j'eIg5cqb-j:e5 2b3boc9c!c#c$cZdei0d=j`eRg)c`j}ebf2d6b0g9dckgfhkiflkvb!d#dxijfkflf.cmf5gnfofzi%d)dvkDf%g/cxbBkMf6 9b!bDc?c@c[c]c.dGkSfIkUf+g{cOkXfTkZfYk1f3k3f8k5f%k7f+k9f:k#f

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~dcefeielexh?d/iNbObX HjNjNe0clbvgUj@hOd6j|h}h1e2e3e4eSd(jVd6c.j2b%c[e?jSg{j~e*csb1gdkik!dnkBiCipfqfrfsf'dwk*d:cCk9b^c(gJk,gPkUkZk4k9k'k,k;k

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|daedegejemeNbOb@d:iIjOjOe1cmbwgVj[hPd7j|h~h5e6e7e8eTd)jWd7c/j3b'c]e@jTg|jaf+ctb2gekjk#dokBiDitfufvfwf(dxk+d;cDk!b_c)gKk-gQkVk0k5k!k(k-k=k

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) 2EAFA2q,rDuGAEuxl]iyl^izlAl3q~cadbd;d8 9 ! + $b%b'bOc4q5q6q7q8q9qBlCl_i{d|d`iod}dChDhEhFhJlKl{i~dae|ipdbeGhHhIhJhRl}iSl~iTlUlVlajWlbjXlYlZl0lcjcededjqdeeKhLhMhNh7l8lejfegefjrdheOhPhQhRh(l)lgjiejehjsdkeShThUhVh:l;lijlemejjtdneWhXhYhZh_lkj`llj{l|l}lmj~lnjambmcmojdmpjemfm[k!qcd?d@dAhenGjJjKe*hmnMjPjMe+hWbNeOeQjogpgqgDdPe,hrgsgQeEdFdYb2c/hugxgLdygxnTjWjUe;hXj?h]hNdzg4jobOdPd^hVeWeXe4cYeAgZe0e5j`h{hRdBgpbSdTd9e!e,iUdCg#e$eIn'j*j'eaibiIgJg5c,e8cqbkcTn-j:j:eci5 2b3boc9c!c#c$c= %c'cYd;e=eZd?e@e;jeifi0dNg3n=j[j`egihiRgUg)c{e!n`j}j}eoi4b~eaf~jVgWgXg1dbfpiYgZgcf2d3d6b,cti0g3g9d4g.nckfkgfvi[nhkkkifwilkvb!d#dxijfkflf.cmf5gnfofmkziAi%d6gwb'd(dxfyfzf)d7gAfBf~nvkykDfEiFi%g'g/cIf=cxbzckoBkEkMfGi6 9b!bDc?c@c[c]c^ ^c_c-dNfOf.dPfQfroGkHkSfKitoIkLkUfNiOi+g.g{cVfBoOkRkXfViIoTkWkZfWiPoYk1k1fXiWo3k6k3fYi2o8k#k5fZi9o%k)k7f0i(o+k.k9f1i/o:k?k#f2i

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) 20L1L2L3L4L5L6L7L8L9L!L#L$L%L'L(L)L*L+L,L-L.L/L^x_x`x{x|x}x~xaybycydy

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) 22q3q~cadbd;d8 9 ! + $b%b'bOc`i|idjfjhjjj-rAhJjPjQjFdxgWj]h^h{hpbSdTd9e!e,iUdCg#e$e*jJg8c:jfi[jUg}j~j3d3gfkkkxiAiwb'd(dxfyfzf)d7gAfBfyk'g=cEkHkLk.gRkWk1k6k#k)k.k?k

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) 1#$%

975  

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

977 return cydriver._cuDeviceGetGraphMemAttribute(device, attr, value) 2# $ % Ah

978  

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

980 return cydriver._cuDeviceSetGraphMemAttribute(device, attr, value) 1#$%

981  

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

983 return cydriver._cuGraphClone(phGraphClone, originalGraph) 2NbN _

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) 2ZL0L1L2L3L4L5L6L7L8L9L!L#L$L%L'L(L)L*L+L,L-L.L/L^x_x`x{x|x}x~x:Laybycydyk2l2m2n2o2p2q2r2s2t2u2v2w2x2y2z2A2B2C2EbFbGbHb(b)b-ib

990  

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

992 return cydriver._cuGraphNodeGetContainingGraph(hNode, phGraph) 2*r

993  

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

995 return cydriver._cuGraphNodeGetLocalId(hNode, nodeId) 2@x

996  

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

998 return cydriver._cuGraphNodeGetToolsId(hNode, toolsNodeId) 2[x

999  

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

1001 return cydriver._cuGraphGetId(hGraph, graphId) 2XL

1002  

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

1004 return cydriver._cuGraphExecGetId(hGraphExec, graphId) 2@i

1005  

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

1007 return cydriver._cuGraphGetNodes(hGraph, nodes, numNodes) 2Ix[iZL0L1LD22L3L4LE2F2G25L6L7L8L9L!LH2I2J2K2L2M2N2O2P2#L$LQ2%L'L(L)LR2S2T2U2*L+L,L-L.L/LV2W2X2Y2Z2021222?xgphpipjpEbFbGbHb(b)b-iO M B C D b =b

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) 232425262728292[iO M B C D b =b)r

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) 22q3q[i7q8q9q5i^x_x!2`x{x|x}x#2$2%2'2~x:Laybycydy(2)2*2+2,2-2.2/2[kX C rlslb )r+r

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) 2[i^x_x`x{x|x}x~x:Laybycydy:2;2=2?2@2[2B D :prlslb vlwl+r

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) 2[iB C D :prlslb vl=bwl

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) 2D :prlslb

1026  

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

1028 return cydriver._cuGraphDestroyNode(hNode) 2=xM B C =bYL

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) 2NbN _ @iAh} ]x

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) 2LbMbagS T 7 2 * zbc d e f g h i j k l m n o p q r s t u v H I J K hd~cadbd;d3 /bidjdAbBbCb#bDb8 9 ! + $b%b'bOcXYYYZY4q5q6q=dcd:b;bObL X ` 0 O M B C D b ,b-b.bkdldmdx y z E w F P Q R PbQbRb# $ % G Y Z Ib*b+bQc

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) 2T * hd~cadbd3 /bidjdAbBbCbDb8 9 ! $b%b'b:b;b0 x y z E w F P Q R PbQbRb# $ %

1074  

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

1076 return cydriver._cuGraphLaunch(hGraphExec, hStream) 2LbMbS T 2 * c d e f g h i j k l m n o p q r s t u v H I J K hd~cadbd;d3 /bidjdAbBbCb#bDb8 9 ! + $b%b'bOccd:b;bNbObL N X _ ` 0 O M B C D b x y z E w F P Q R PbQbRb# $ % G Y Z Ah}

1077  

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

1079 return cydriver._cuGraphExecDestroy(hGraphExec) 2LbMbagS T 7 2 * zbc d e f g h i j k l m n o p q r s t u v H I J K hd~cadbd;d3 /bidjdAbBbCb#bDb8 9 ! + $b%b'bOcXYYYZY4q5q6q=dcd:b;bObL X ` 0 O M B C D b ,b-b.bkdldmdx y z E w F P Q R PbQbRb# $ % G Y Z Ib*b+bQc@i} ]x

1080  

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

1082 return cydriver._cuGraphDestroy(hGraph) 2LbMbagS T .i7 2 * zbc d e f g h i j k l m n o p q r s t u v H I J K rCsCtCuCvCwCxCyCzCACBCCCDCECFCGCHCICJCKCLC[iMCNCOCPC3 QC4uRCSCTCUCVCWCXCYCZC0C1C2C3C4C5C6C7C8C9C!C#C$C%C'C(C)C*C+C?b,C5u6u-C.C/C:C;C=C?C@C[C]C^C_C`C{C@b|C7u8u}C~CaDbDcDdDeDfDgDhDiDjDkDlDmDnDoDpDqDrDsDtDuDvDwDxDyD[bzDAD9u!uBDCDDDEDFDGDHDIDJDKDLDMDNDODPD]bQDRD#u$uSDTDUDVDWDXDYDZD0D1D2D3D4D5D6D^b7D8D%u'u9D!D#D$D%D'D(D)D*D+D,D-D.D/D:D_b;D=D(u)u?D@D[D]D^D_D`D{D|D}D~DaEbEcEdEeEfEgEhEiEjEkElEmEnE=xoEpEqErEsEtEtlRYSYTYUYJxVY?x-r[k!q=dulcdgphpipjpEbFbGbHb:b;b(bxh?d/iNbOb@d:iL N |fX _ ` )b0 -iO M B C D VL:prlslb vl=bwl,b-b.bkdldmdx y z E w F P Q R PbQbRb# $ % G Y Z Ib*b+bddQcU @i)rXL*r+r@x[xAh} WYPEccRESETE*u+uVEWEXEYEZE0E1E2E3E5E6E9Edc#E$E%E,u-u(E)E*E+E,E-E.E/E:E=E?EWb@E.u/u[E]E^E_E`E{E|E}E~E:u( ;u=u?u]q^q@u[u]u^u_u`u{u|u}u~uavlbbvmbcvZbdF. eF/ fF: gF; hFiFnbjFkFdvevlFmFnFoFpFqFrFsFtFuFvFecxFyFzFfvgvAFBFCFDFEFFFGFHFIFJFKFLF0bNFOFPFhvivRFSFTFUFVFWFXFYFZF1F2F3Fob4Fjvkv5F6F7F8F9F!F#F$F%Flv1bnvovpvqvrvsvtvuvvvwvxvyvzvAvBvCvDvEvFvGvHvIvJvKvLvMvNvpb+FOvPv,F-F.F/F:F;F=F?Ffc@F[F]FQvRv^F_F`F{F|F}F~FaGbGcGdGeGfGgGhGiGjGkGlGmGgcnGoGpGSvTvqGrGsGtGuGvGwGxGyGzGAGhcBGUvVvCGDGEGFGGGHGIGJGKGncLGMGNGWvXvOGPGQGRGSGTGUGVGWGXGYG5 ZGYvZv0G1G2G3G4G= 5G0v1v6G7G8G9G!G#G$Gpc%G'G(G2v3v)G*G+G,G-G.G/G:G;G=G?G@Gqc[G]G4v5v^G_G`G{G|G}G~GaHbH6vrb8v9v!v_q`q$v%v'v(v)v*v+v,v-v.v/vgHhHrcjHkHlH:v;vnHoHpHqHrHsHtHuHvHxHyH4bzH=v?vAHBHCHDHEHFHGHHHIH@v) [v]v^v{q|q_v`v{v|v}v~vawbwcwdwewsbfwtbgw7bMH? NH@ OH[ PH] QHRHubSHTHhwiwUHVHWHXHYHZH0H1H2H3H4Hsc6H7H8Hjwkw9H!H#H$H%H'H(H)H*H+H,H-Htc/H:H;Hlwmw?H@H[H]H^H_H`H{H|H~HaIbIvbcInwowdIeIfIgIhIiIjIkIlIpw8brwswtwuwvwwwxwywzwAwBwCwDwEwFwGwHwIwJwKwLwMwNwOwPwQwRwwbqISwTwrIsItIuIvIwIxIyIuczIAIBIUwVwCIDIEIFIGIHIIIJIKILIMINIOIPIQIRISITIUIVIvcWIXIYIWwXwZI0I1I2I3I4I5I6I7I8I9Iwc!IYwZw#I$I%I'I(I)I*I+I,ICc-I.I/I0w1w:I;I=I?I@I[I]I^I_I`I{I6 |I2w3w}I~IaJbJcJ^ dJ4w5weJfJgJhJiJjJkJEclJmJnJ6w7woJpJqJrJsJtJuJvJwJxJyJzJFcAJBJ8w9wCJDJEJFJGJHJIJJJKJ!wyb$w%w'w}q~q)w*w+w,w-w.w/w:w;w=w?wPJQJGcSJTJUJ@w[wWJXJYJZJ0J1J2J3J4J6J7J8JHc!J#J$J]w^w'J(J)J*J+J,J-J.J/J;J=J?JIc[J]J^J_w`w`J{J|J}J~JaKbKcKdKfKgKhKJcjKkKlK{w|wnKoKpKqKrKsKtKuKvKxKyKzKKcBKCKDK}w~wFKGKHKIKJKKKLKMKNKPKQKRKLcTKUKVKaxbxXKYKZK0K1K2K3K4K5K7K8K9KMc#K$K%Kcxdx(K)K*K+K,K-K.K/K:K=K?K@KNc]K^K_Kexfx{K|K}K~KaLbLcLdLeLgLhL

1083  

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

1085 return cydriver._cuGraphExecUpdate_v2(hGraphExec, hGraph, resultInfo) 2G Y Z Ib

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) 2DuEuU

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) 2LbMbhd3 /bidjdAbBbCb#bDb5i@k?b{d|dDlElod@b~daeLlMlpd[bcede1l2lqd]bfege9l!lrd^bieje*l+lsd_bleme=l?ltd=dEbFbGbHb:b;b(bxh?d/iNbOb@d:iL N |fX _ ` )b0 O M B C D b Z ccHjIjfnJedcNjOjnnLeWbNeOeogDd( 0c1cGdXblbmbZb. / : ; nbvgwg:h3cecUjVjynTe0b@h[hYjMdobOdPdVe4c1b6j7j8jQd|h}h1e2e3e4e~h5e6e7e8epbSdTd9efc(j)jJn%eDgEgFgGggcVdWd(e+ehc6c7c8cXdicjcqbkclcmcnc.j/jUn/e5 2b3boc= %c'cYdpc[e]eKg^eqc?j@j4n_erbSgTgii(crc{j|j#n|e4b~eafVg1d) *c+c4d5bsbtb7b? @ [ ] ub1g2gui-cscdkek/nfftcikjk]nhfvb!d#djf.c8bnkokpk$dBiCipfqfrfsfDitfufvfwfwb'd(dxfucwkxkaoCf8g9g!g#gvc*d+dEfHfwc:c;c=c,dxcycxbzcAcBcCcCkDkloLf6 9b!bDc^ ^c_c-dEc(g)gHiRfFcJkKkuoTfyb,g-gPi`cGcPkQkCoWfHcUkVkJoYfIcZk0kQo0fJc4k5kXo2fKc9k!k3o4fLc'k(kdr6fMc,k-k)o8fNc;k=k:o!f

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) 2LbMbhd3 /bidjdAbBbCb#bDb5i@k?b{d|dDlElod@b~daeLlMlpd[bcede1l2lqd]bfege9l!lrd^bieje*l+lsd_bleme=l?ltd=dEbFbGbHb:b;b(bxh?d/iNbOb@d:iL N |fX _ ` )b0 O M B C D b Z ccHjIjfnJedcNjOjnnLeWbNeOeogDd( 0c1cGdXblbmbZb. / : ; nbvgwg:h3cecUjVjynTe0b@h[hYjMdobOdPdVe4c1b6j7j8jQd|h}h1e2e3e4e~h5e6e7e8epbSdTd9efc(j)jJn%eDgEgFgGggcVdWd(e+ehc6c7c8cXdicjcqbkclcmcnc.j/jUn/e5 2b3boc= %c'cYdpc[e]eKg^eqc?j@j4n_erbSgTgii(crc{j|j#n|e4b~eafVg1d) *c+c4d5bsbtb7b? @ [ ] ub1g2gui-cscdkek/nfftcikjk]nhfvb!d#djf.c8bnkokpk$dBiCipfqfrfsfDitfufvfwfwb'd(dxfucwkxkaoCf8g9g!g#gvc*d+dEfHfwc:c;c=c,dxcycxbzcAcBcCcCkDkloLf6 9b!bDc^ ^c_c-dEc(g)gHiRfFcJkKkuoTfyb,g-gPi`cGcPkQkCoWfHcUkVkJoYfIcZk0kQo0fJc4k5kXo2fKc9k!k3o4fLc'k(kdr6fMc,k-k)o8fNc;k=k:o!f

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 r s t u v H I J K IxFlGlHlIlNlOlPlQl3l4l5l6l#l$l%l'l,l-l.l/l@l[l]l^ltlulgphpipjpEbFbGbHb-iG U WL*r} gnhnjnknonpnrnsnpgqgrgsgHdIdJdKd. / : ; tnunvnwnznAnCnDnZj0j2j3jWeXeZe0e9j!j$j%j1e2e3e4e5e6e7e8e!e,i#e$eKnLnMnNnDgEgFgGgOnPnQnRnSn)e*e-e.eicjclcmcVnWnYnZn9c!c#c$c;e=e?e@eLgMgOgPg5n6n7n8njikimini9n$n%n(n)nWgXgYgZg5d6d7d8d? @ [ ] *n+n,n-n:n;n?n@n^n_n{n|nkflfnfofqkrktkukpfqfrfsftfufvfwfyfzfAfBfbocodoeo8g9g!g#gfogohoiojoFfGfJfKfxcycAcBcmonopoqo?c@c[c]cNfOfPfQfIiJiLiMivowoxoyoQiRiTiUiAoDoEoGoHoKoLoNoOoRoSoUoVoYocr0o1o4o5o7o8o!o#o%o'o*o+o-o.o;o=o@o[o

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) 2-i

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 r s t u v H I J K IxFlGlHlIlNlOlPlQl3l4l5l6l#l$l%l'l,l-l.l/l@l[l]l^ltlJxulgphpipjpEbFbGbHb-iG U WLlqgnhnjnknnqonpnrnsnpgqgrgsgReHdIdJdKd. / : ; /hnbugvgwgxg:htnun3cLdygpqvnwnqqznAnCnDnEnZj0j2j3jWeXeZe0eGn9j!j$j%j1e2e3e4e5e6e7e8e!e,i#e$etqKnLnMnNnDgEgFgGgOnPnQnRnSnHg)e*e-e.eicjclcmcuqVnWnYnZn9c!c#c$c;e=e?e@ediLgMgOgPg5n6n7n8n]jjikimini9nzq$n%n(n)nWgXgYgZgdf5d6d7d8d? @ [ ] tiub0g1g2g3gui*n+n-c9d4gBq,n-nCq:n;n?n@nDq^n_n{n|nkflfnfof}nqkrktkukpfqfrfsftfufvfwfyfzfAfBfFqbocodoeo8g9g!g#gfogohoiojo$gFfGfJfKfxcycAcBcGqmonopoqo?c@c[c]cNfOfPfQfFkIiJiLiMivowoxoyoMkQiRiTiUiAoMqDoEoGoHoQqKoLoNoOoSqRoSoUoVoUqYocr0o1oWq4o5o7o8oYq!o#o%o'o0q*o+o-o.o1q;o=o@o[o

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^dKuLuMuNuOuPuQuRuSuTuUuVuWuXuYuZu0u1u

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`B{B|B}B~BaCbCcCdCeCfCgChCiCjCkClCmCnCoCpC

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?B@B[B]B^B_B

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) 2db?g@g[gep0Y1Y2Y3Y4Y5Y]g^g_g(i6Y`g{g7Y|g;x8Y9Y!Y

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) 2?gdp@g[g]g^g_g(i`g{g|g{k

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) 2?gdp@g[g]g^g_g(i`g{g|g{k

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?g@g[g]g^g_g(i`g{g|g{k;x

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#Y

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#Y

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) 2~kujvjueV W wjxjyjzjAjBj

1341  

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

1343 return cydriver._cuGreenCtxDestroy(hCtx) 2~kGEHEIEV W JEKELEMENEOE

1344  

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

1346 return cydriver._cuCtxFromGreenCtx(pContext, hCtx) 2~kujvjueV W wjxjyjzjAjBj

1347  

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

1349 return cydriver._cuDeviceGetDevResource(device, resource, typename) 2$Y%YMzujvjuemmnmwjxjyjzjAjBjNzOzPzQzRzSzTzUzVzWzXzYzZz0z1z2z3z4z

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) 2~k]29x

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%Y

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) 2$Y~kujvjueV W wjxjyjzjAjBj^2_2`2{2|2}2~2

1362  

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

1364 return cydriver._cuDevResourceGenerateDesc(phDesc, resources, nbResources) 2~kujvjueV W wjxjyjzjAjBj

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) 29xJbV W sYQL?i

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) 2UL

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) 2a3

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'Y

1419  

1420cdef CUresult cuProfilerStop() except ?CUDA_ERROR_NOT_FOUND nogil: 

1421 return cydriver._cuProfilerStop() 2'Y

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) 2?gdp@g[gep0Y1Y2Y3Y4Y]g^g_g(i6Y`g{g7Y|g{k;x8Y9Y!Y

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) 25Y

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)