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
« 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
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
7cdef CUresult cuGetErrorString(CUresult error, const char** pStr) except ?CUDA_ERROR_NOT_FOUND nogil:
8 return cydriver._cuGetErrorString(error, pStr) 2;Ley=L
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
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
16cdef CUresult cuDriverGetVersion(int* driverVersion) except ?CUDA_ERROR_NOT_FOUND nogil:
17 return cydriver._cuDriverGetVersion(driverVersion) 2a *Y+Y,Y-Y.Y/Y
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
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
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
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
31cdef CUresult cuDeviceGetLuid(char* luid, unsigned int* deviceNodeMask, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
32 return cydriver._cuDeviceGetLuid(luid, deviceNodeMask, dev)
34cdef CUresult cuDeviceTotalMem(size_t* numbytes, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
35 return cydriver._cuDeviceTotalMem_v2(numbytes, dev)
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)
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
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)
46cdef CUresult cuDeviceGetNvSciSyncAttributes(void* nvSciSyncAttrList, CUdevice dev, int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
47 return cydriver._cuDeviceGetNvSciSyncAttributes(nvSciSyncAttrList, dev, flags)
49cdef CUresult cuDeviceSetMemPool(CUdevice dev, CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil:
50 return cydriver._cuDeviceSetMemPool(dev, pool) 20P
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
55cdef CUresult cuDeviceGetDefaultMemPool(CUmemoryPool* pool_out, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
56 return cydriver._cuDeviceGetDefaultMemPool(pool_out, dev) 20P
58cdef CUresult cuDeviceGetExecAffinitySupport(int* pi, CUexecAffinityType typename, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
59 return cydriver._cuDeviceGetExecAffinitySupport(pi, typename, dev)
61cdef CUresult cuFlushGPUDirectRDMAWrites(CUflushGPUDirectRDMAWritesTarget target, CUflushGPUDirectRDMAWritesScope scope) except ?CUDA_ERROR_NOT_FOUND nogil:
62 return cydriver._cuFlushGPUDirectRDMAWrites(target, scope)
64cdef CUresult cuDeviceGetProperties(CUdevprop* prop, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
65 return cydriver._cuDeviceGetProperties(prop, dev)
67cdef CUresult cuDeviceComputeCapability(int* major, int* minor, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
68 return cydriver._cuDeviceComputeCapability(major, minor, dev)
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
73cdef CUresult cuDevicePrimaryCtxRelease(CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
74 return cydriver._cuDevicePrimaryCtxRelease_v2(dev) 2cZdZeZfZgZhZiZjZkZlZmZnZoZpZqZrZsZtZuZvZwZxZyZzZAZBZ=pCZDZ
76cdef CUresult cuDevicePrimaryCtxSetFlags(CUdevice dev, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
77 return cydriver._cuDevicePrimaryCtxSetFlags_v2(dev, flags)
79cdef CUresult cuDevicePrimaryCtxGetState(CUdevice dev, unsigned int* flags, int* active) except ?CUDA_ERROR_NOT_FOUND nogil:
80 return cydriver._cuDevicePrimaryCtxGetState(dev, flags, active)
82cdef CUresult cuDevicePrimaryCtxReset(CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
83 return cydriver._cuDevicePrimaryCtxReset_v2(dev)
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
88cdef CUresult cuCtxDestroy(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
89 return cydriver._cuCtxDestroy_v2(ctx) 2EZFZGZHZIZJZKZLZMZNZOZPZQZRZSZTZUZVZWZXZYZZZ0Z1Z2Z3Z4Z5Z6Z7Z8Z9Z!Z#Z$Z
91cdef CUresult cuCtxPushCurrent(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
92 return cydriver._cuCtxPushCurrent_v2(ctx) 2qC2P
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
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
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
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
106cdef CUresult cuCtxGetDevice_v2(CUdevice* device, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
107 return cydriver._cuCtxGetDevice_v2(device, ctx)
109cdef CUresult cuCtxGetFlags(unsigned int* flags) except ?CUDA_ERROR_NOT_FOUND nogil:
110 return cydriver._cuCtxGetFlags(flags)
112cdef CUresult cuCtxSetFlags(unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
113 return cydriver._cuCtxSetFlags(flags)
115cdef CUresult cuCtxGetId(CUcontext ctx, unsigned long long* ctxId) except ?CUDA_ERROR_NOT_FOUND nogil:
116 return cydriver._cuCtxGetId(ctx, ctxId)
118cdef CUresult cuCtxSynchronize() except ?CUDA_ERROR_NOT_FOUND nogil:
119 return cydriver._cuCtxSynchronize()
121cdef CUresult cuCtxSynchronize_v2(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
122 return cydriver._cuCtxSynchronize_v2(ctx)
124cdef CUresult cuCtxSetLimit(CUlimit limit, size_t value) except ?CUDA_ERROR_NOT_FOUND nogil:
125 return cydriver._cuCtxSetLimit(limit, value)
127cdef CUresult cuCtxGetLimit(size_t* pvalue, CUlimit limit) except ?CUDA_ERROR_NOT_FOUND nogil:
128 return cydriver._cuCtxGetLimit(pvalue, limit)
130cdef CUresult cuCtxGetCacheConfig(CUfunc_cache* pconfig) except ?CUDA_ERROR_NOT_FOUND nogil:
131 return cydriver._cuCtxGetCacheConfig(pconfig)
133cdef CUresult cuCtxSetCacheConfig(CUfunc_cache config) except ?CUDA_ERROR_NOT_FOUND nogil:
134 return cydriver._cuCtxSetCacheConfig(config)
136cdef CUresult cuCtxGetApiVersion(CUcontext ctx, unsigned int* version) except ?CUDA_ERROR_NOT_FOUND nogil:
137 return cydriver._cuCtxGetApiVersion(ctx, version)
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
142cdef CUresult cuCtxResetPersistingL2Cache() except ?CUDA_ERROR_NOT_FOUND nogil:
143 return cydriver._cuCtxResetPersistingL2Cache()
145cdef CUresult cuCtxGetExecAffinity(CUexecAffinityParam* pExecAffinity, CUexecAffinityType typename) except ?CUDA_ERROR_NOT_FOUND nogil:
146 return cydriver._cuCtxGetExecAffinity(pExecAffinity, typename)
148cdef CUresult cuCtxRecordEvent(CUcontext hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
149 return cydriver._cuCtxRecordEvent(hCtx, hEvent)
151cdef CUresult cuCtxWaitEvent(CUcontext hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
152 return cydriver._cuCtxWaitEvent(hCtx, hEvent)
154cdef CUresult cuCtxAttach(CUcontext* pctx, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
155 return cydriver._cuCtxAttach(pctx, flags)
157cdef CUresult cuCtxDetach(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
158 return cydriver._cuCtxDetach(ctx)
160cdef CUresult cuCtxGetSharedMemConfig(CUsharedconfig* pConfig) except ?CUDA_ERROR_NOT_FOUND nogil:
161 return cydriver._cuCtxGetSharedMemConfig(pConfig)
163cdef CUresult cuCtxSetSharedMemConfig(CUsharedconfig config) except ?CUDA_ERROR_NOT_FOUND nogil:
164 return cydriver._cuCtxSetSharedMemConfig(config)
166cdef CUresult cuModuleLoad(CUmodule* module, const char* fname) except ?CUDA_ERROR_NOT_FOUND nogil:
167 return cydriver._cuModuleLoad(module, fname)
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
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
175cdef CUresult cuModuleLoadFatBinary(CUmodule* module, const void* fatCubin) except ?CUDA_ERROR_NOT_FOUND nogil:
176 return cydriver._cuModuleLoadFatBinary(module, fatCubin)
178cdef CUresult cuModuleUnload(CUmodule hmod) except ?CUDA_ERROR_NOT_FOUND nogil:
179 return cydriver._cuModuleUnload(hmod) 2[d]d6i7i8i}f9i!i
181cdef CUresult cuModuleGetLoadingMode(CUmoduleLoadingMode* mode) except ?CUDA_ERROR_NOT_FOUND nogil:
182 return cydriver._cuModuleGetLoadingMode(mode)
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
187cdef CUresult cuModuleGetFunctionCount(unsigned int* count, CUmodule mod) except ?CUDA_ERROR_NOT_FOUND nogil:
188 return cydriver._cuModuleGetFunctionCount(count, mod)
190cdef CUresult cuModuleEnumerateFunctions(CUfunction* functions, unsigned int numFunctions, CUmodule mod) except ?CUDA_ERROR_NOT_FOUND nogil:
191 return cydriver._cuModuleEnumerateFunctions(functions, numFunctions, mod)
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
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)
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)
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)
205cdef CUresult cuLinkComplete(CUlinkState state, void** cubinOut, size_t* sizeOut) except ?CUDA_ERROR_NOT_FOUND nogil:
206 return cydriver._cuLinkComplete(state, cubinOut, sizeOut)
208cdef CUresult cuLinkDestroy(CUlinkState state) except ?CUDA_ERROR_NOT_FOUND nogil:
209 return cydriver._cuLinkDestroy(state)
211cdef CUresult cuModuleGetTexRef(CUtexref* pTexRef, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
212 return cydriver._cuModuleGetTexRef(pTexRef, hmod, name)
214cdef CUresult cuModuleGetSurfRef(CUsurfref* pSurfRef, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
215 return cydriver._cuModuleGetSurfRef(pSurfRef, hmod, name)
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
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
223cdef CUresult cuLibraryUnload(CUlibrary library) except ?CUDA_ERROR_NOT_FOUND nogil:
224 return cydriver._cuLibraryUnload(library)
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
229cdef CUresult cuLibraryGetKernelCount(unsigned int* count, CUlibrary lib) except ?CUDA_ERROR_NOT_FOUND nogil:
230 return cydriver._cuLibraryGetKernelCount(count, lib)
232cdef CUresult cuLibraryEnumerateKernels(CUkernel* kernels, unsigned int numKernels, CUlibrary lib) except ?CUDA_ERROR_NOT_FOUND nogil:
233 return cydriver._cuLibraryEnumerateKernels(kernels, numKernels, lib)
235cdef CUresult cuLibraryGetModule(CUmodule* pMod, CUlibrary library) except ?CUDA_ERROR_NOT_FOUND nogil:
236 return cydriver._cuLibraryGetModule(pMod, library)
238cdef CUresult cuKernelGetFunction(CUfunction* pFunc, CUkernel kernel) except ?CUDA_ERROR_NOT_FOUND nogil:
239 return cydriver._cuKernelGetFunction(pFunc, kernel)
241cdef CUresult cuKernelGetLibrary(CUlibrary* pLib, CUkernel kernel) except ?CUDA_ERROR_NOT_FOUND nogil:
242 return cydriver._cuKernelGetLibrary(pLib, kernel)
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)
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)
250cdef CUresult cuLibraryGetUnifiedFunction(void** fptr, CUlibrary library, const char* symbol) except ?CUDA_ERROR_NOT_FOUND nogil:
251 return cydriver._cuLibraryGetUnifiedFunction(fptr, library, symbol)
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
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)
259cdef CUresult cuKernelSetCacheConfig(CUkernel kernel, CUfunc_cache config, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
260 return cydriver._cuKernelSetCacheConfig(kernel, config, dev)
262cdef CUresult cuKernelGetName(const char** name, CUkernel hfunc) except ?CUDA_ERROR_NOT_FOUND nogil:
263 return cydriver._cuKernelGetName(name, hfunc) 2{1
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
268cdef CUresult cuKernelGetParamCount(CUkernel kernel, size_t* paramCount) except ?CUDA_ERROR_NOT_FOUND nogil:
269 return cydriver._cuKernelGetParamCount(kernel, paramCount)
271cdef CUresult cuMemGetInfo(size_t* free, size_t* total) except ?CUDA_ERROR_NOT_FOUND nogil:
272 return cydriver._cuMemGetInfo_v2(free, total)
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
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)
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
283cdef CUresult cuMemGetAddressRange(CUdeviceptr* pbase, size_t* psize, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
284 return cydriver._cuMemGetAddressRange_v2(pbase, psize, dptr)
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
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
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
295cdef CUresult cuMemHostGetDevicePointer(CUdeviceptr* pdptr, void* p, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
296 return cydriver._cuMemHostGetDevicePointer_v2(pdptr, p, Flags)
298cdef CUresult cuMemHostGetFlags(unsigned int* pFlags, void* p) except ?CUDA_ERROR_NOT_FOUND nogil:
299 return cydriver._cuMemHostGetFlags(pFlags, p)
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
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)
307cdef CUresult cuDeviceUnregisterAsyncNotification(CUdevice device, CUasyncCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil:
308 return cydriver._cuDeviceUnregisterAsyncNotification(device, callback)
310cdef CUresult cuDeviceGetByPCIBusId(CUdevice* dev, const char* pciBusId) except ?CUDA_ERROR_NOT_FOUND nogil:
311 return cydriver._cuDeviceGetByPCIBusId(dev, pciBusId)
313cdef CUresult cuDeviceGetPCIBusId(char* pciBusId, int length, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
314 return cydriver._cuDeviceGetPCIBusId(pciBusId, length, dev)
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
319cdef CUresult cuIpcOpenEventHandle(CUevent* phEvent, CUipcEventHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil:
320 return cydriver._cuIpcOpenEventHandle(phEvent, handle)
322cdef CUresult cuIpcGetMemHandle(CUipcMemHandle* pHandle, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
323 return cydriver._cuIpcGetMemHandle(pHandle, dptr)
325cdef CUresult cuIpcOpenMemHandle(CUdeviceptr* pdptr, CUipcMemHandle handle, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
326 return cydriver._cuIpcOpenMemHandle_v2(pdptr, handle, Flags)
328cdef CUresult cuIpcCloseMemHandle(CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
329 return cydriver._cuIpcCloseMemHandle(dptr)
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
334cdef CUresult cuMemHostUnregister(void* p) except ?CUDA_ERROR_NOT_FOUND nogil:
335 return cydriver._cuMemHostUnregister(p) 2jqFx
337cdef CUresult cuMemcpy(CUdeviceptr dst, CUdeviceptr src, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
338 return cydriver._cuMemcpy(dst, src, ByteCount)
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)
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}
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}
349cdef CUresult cuMemcpyDtoD(CUdeviceptr dstDevice, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
350 return cydriver._cuMemcpyDtoD_v2(dstDevice, srcDevice, ByteCount)
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)
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)
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)
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)
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)
367cdef CUresult cuMemcpy2D(const CUDA_MEMCPY2D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil:
368 return cydriver._cuMemcpy2D_v2(pCopy)
370cdef CUresult cuMemcpy2DUnaligned(const CUDA_MEMCPY2D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil:
371 return cydriver._cuMemcpy2DUnaligned_v2(pCopy)
373cdef CUresult cuMemcpy3D(const CUDA_MEMCPY3D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil:
374 return cydriver._cuMemcpy3D_v2(pCopy)
376cdef CUresult cuMemcpy3DPeer(const CUDA_MEMCPY3D_PEER* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil:
377 return cydriver._cuMemcpy3DPeer(pCopy)
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
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)
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)
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
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)
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)
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)
400cdef CUresult cuMemcpy2DAsync(const CUDA_MEMCPY2D* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
401 return cydriver._cuMemcpy2DAsync_v2(pCopy, hStream)
403cdef CUresult cuMemcpy3DAsync(const CUDA_MEMCPY3D* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
404 return cydriver._cuMemcpy3DAsync_v2(pCopy, hStream)
406cdef CUresult cuMemcpy3DPeerAsync(const CUDA_MEMCPY3D_PEER* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
407 return cydriver._cuMemcpy3DPeerAsync(pCopy, hStream)
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)
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)
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)
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)
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)
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)
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)
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)
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)
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)
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
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
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
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)
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)
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)
457cdef CUresult cuArrayCreate(CUarray* pHandle, const CUDA_ARRAY_DESCRIPTOR* pAllocateArray) except ?CUDA_ERROR_NOT_FOUND nogil:
458 return cydriver._cuArrayCreate_v2(pHandle, pAllocateArray) 2NY
460cdef CUresult cuArrayGetDescriptor(CUDA_ARRAY_DESCRIPTOR* pArrayDescriptor, CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil:
461 return cydriver._cuArrayGetDescriptor_v2(pArrayDescriptor, hArray)
463cdef CUresult cuArrayGetSparseProperties(CUDA_ARRAY_SPARSE_PROPERTIES* sparseProperties, CUarray array) except ?CUDA_ERROR_NOT_FOUND nogil:
464 return cydriver._cuArrayGetSparseProperties(sparseProperties, array)
466cdef CUresult cuMipmappedArrayGetSparseProperties(CUDA_ARRAY_SPARSE_PROPERTIES* sparseProperties, CUmipmappedArray mipmap) except ?CUDA_ERROR_NOT_FOUND nogil:
467 return cydriver._cuMipmappedArrayGetSparseProperties(sparseProperties, mipmap)
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)
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)
475cdef CUresult cuArrayGetPlane(CUarray* pPlaneArray, CUarray hArray, unsigned int planeIdx) except ?CUDA_ERROR_NOT_FOUND nogil:
476 return cydriver._cuArrayGetPlane(pPlaneArray, hArray, planeIdx)
478cdef CUresult cuArrayDestroy(CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil:
479 return cydriver._cuArrayDestroy(hArray) 2NY
481cdef CUresult cuArray3DCreate(CUarray* pHandle, const CUDA_ARRAY3D_DESCRIPTOR* pAllocateArray) except ?CUDA_ERROR_NOT_FOUND nogil:
482 return cydriver._cuArray3DCreate_v2(pHandle, pAllocateArray)
484cdef CUresult cuArray3DGetDescriptor(CUDA_ARRAY3D_DESCRIPTOR* pArrayDescriptor, CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil:
485 return cydriver._cuArray3DGetDescriptor_v2(pArrayDescriptor, hArray)
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)
490cdef CUresult cuMipmappedArrayGetLevel(CUarray* pLevelArray, CUmipmappedArray hMipmappedArray, unsigned int level) except ?CUDA_ERROR_NOT_FOUND nogil:
491 return cydriver._cuMipmappedArrayGetLevel(pLevelArray, hMipmappedArray, level)
493cdef CUresult cuMipmappedArrayDestroy(CUmipmappedArray hMipmappedArray) except ?CUDA_ERROR_NOT_FOUND nogil:
494 return cydriver._cuMipmappedArrayDestroy(hMipmappedArray)
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)
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)
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
505cdef CUresult cuMemAddressFree(CUdeviceptr ptr, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil:
506 return cydriver._cuMemAddressFree(ptr, size) 2edfd~ abgd
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
511cdef CUresult cuMemRelease(CUmemGenericAllocationHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil:
512 return cydriver._cuMemRelease(handle) 2edfd~ abgd
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
517cdef CUresult cuMemMapArrayAsync(CUarrayMapInfo* mapInfoList, unsigned int count, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
518 return cydriver._cuMemMapArrayAsync(mapInfoList, count, hStream)
520cdef CUresult cuMemUnmap(CUdeviceptr ptr, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil:
521 return cydriver._cuMemUnmap(ptr, size) 2edfd~ abgd
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
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)
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)
532cdef CUresult cuMemImportFromShareableHandle(CUmemGenericAllocationHandle* handle, void* osHandle, CUmemAllocationHandleType shHandleType) except ?CUDA_ERROR_NOT_FOUND nogil:
533 return cydriver._cuMemImportFromShareableHandle(handle, osHandle, shHandleType)
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
538cdef CUresult cuMemGetAllocationPropertiesFromHandle(CUmemAllocationProp* prop, CUmemGenericAllocationHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil:
539 return cydriver._cuMemGetAllocationPropertiesFromHandle(prop, handle)
541cdef CUresult cuMemRetainAllocationHandle(CUmemGenericAllocationHandle* handle, void* addr) except ?CUDA_ERROR_NOT_FOUND nogil:
542 return cydriver._cuMemRetainAllocationHandle(handle, addr) 2edfd~ abgd
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
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# $ %
550cdef CUresult cuMemPoolTrimTo(CUmemoryPool pool, size_t minBytesToKeep) except ?CUDA_ERROR_NOT_FOUND nogil:
551 return cydriver._cuMemPoolTrimTo(pool, minBytesToKeep)
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
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
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
562cdef CUresult cuMemPoolGetAccess(CUmemAccess_flags* flags, CUmemoryPool memPool, CUmemLocation* location) except ?CUDA_ERROR_NOT_FOUND nogil:
563 return cydriver._cuMemPoolGetAccess(flags, memPool, location)
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
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
571cdef CUresult cuMemGetDefaultMemPool(CUmemoryPool* pool_out, CUmemLocation* location, CUmemAllocationType typename) except ?CUDA_ERROR_NOT_FOUND nogil:
572 return cydriver._cuMemGetDefaultMemPool(pool_out, location, typename)
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
577cdef CUresult cuMemSetMemPool(CUmemLocation* location, CUmemAllocationType typename, CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil:
578 return cydriver._cuMemSetMemPool(location, typename, pool)
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
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
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)
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
592cdef CUresult cuMemPoolImportPointer(CUdeviceptr* ptr_out, CUmemoryPool pool, CUmemPoolPtrExportData* shareData) except ?CUDA_ERROR_NOT_FOUND nogil:
593 return cydriver._cuMemPoolImportPointer(ptr_out, pool, shareData)
595cdef CUresult cuMulticastCreate(CUmemGenericAllocationHandle* mcHandle, const CUmulticastObjectProp* prop) except ?CUDA_ERROR_NOT_FOUND nogil:
596 return cydriver._cuMulticastCreate(mcHandle, prop)
598cdef CUresult cuMulticastAddDevice(CUmemGenericAllocationHandle mcHandle, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
599 return cydriver._cuMulticastAddDevice(mcHandle, dev)
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)
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)
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)
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)
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)
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)
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
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
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
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
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
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
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
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
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
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
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
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
655cdef CUresult cuStreamBeginCaptureToCig(CUstream hStream, CUstreamCigCaptureParams* streamCigCaptureParams) except ?CUDA_ERROR_NOT_FOUND nogil:
656 return cydriver._cuStreamBeginCaptureToCig(hStream, streamCigCaptureParams)
658cdef CUresult cuStreamEndCaptureToCig(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
659 return cydriver._cuStreamEndCaptureToCig(hStream)
661cdef CUresult cuStreamGetPriority(CUstream hStream, int* priority) except ?CUDA_ERROR_NOT_FOUND nogil:
662 return cydriver._cuStreamGetPriority(hStream, priority)
664cdef CUresult cuStreamGetDevice(CUstream hStream, CUdevice* device) except ?CUDA_ERROR_NOT_FOUND nogil:
665 return cydriver._cuStreamGetDevice(hStream, device)
667cdef CUresult cuStreamGetFlags(CUstream hStream, unsigned int* flags) except ?CUDA_ERROR_NOT_FOUND nogil:
668 return cydriver._cuStreamGetFlags(hStream, flags)
670cdef CUresult cuStreamGetId(CUstream hStream, unsigned long long* streamId) except ?CUDA_ERROR_NOT_FOUND nogil:
671 return cydriver._cuStreamGetId(hStream, streamId)
673cdef CUresult cuStreamGetCtx(CUstream hStream, CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil:
674 return cydriver._cuStreamGetCtx(hStream, pctx)
676cdef CUresult cuStreamGetCtx_v2(CUstream hStream, CUcontext* pCtx, CUgreenCtx* pGreenCtx) except ?CUDA_ERROR_NOT_FOUND nogil:
677 return cydriver._cuStreamGetCtx_v2(hStream, pCtx, pGreenCtx)
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
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)
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
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
691cdef CUresult cuThreadExchangeStreamCaptureMode(CUstreamCaptureMode* mode) except ?CUDA_ERROR_NOT_FOUND nogil:
692 return cydriver._cuThreadExchangeStreamCaptureMode(mode)
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
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
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
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
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)
709cdef CUresult cuStreamQuery(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
710 return cydriver._cuStreamQuery(hStream)
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
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
718cdef CUresult cuStreamCopyAttributes(CUstream dst, CUstream src) except ?CUDA_ERROR_NOT_FOUND nogil:
719 return cydriver._cuStreamCopyAttributes(dst, src)
721cdef CUresult cuStreamGetAttribute(CUstream hStream, CUstreamAttrID attr, CUstreamAttrValue* value_out) except ?CUDA_ERROR_NOT_FOUND nogil:
722 return cydriver._cuStreamGetAttribute(hStream, attr, value_out)
724cdef CUresult cuStreamSetAttribute(CUstream hStream, CUstreamAttrID attr, const CUstreamAttrValue* value) except ?CUDA_ERROR_NOT_FOUND nogil:
725 return cydriver._cuStreamSetAttribute(hStream, attr, value)
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
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
733cdef CUresult cuEventRecordWithFlags(CUevent hEvent, CUstream hStream, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
734 return cydriver._cuEventRecordWithFlags(hEvent, hStream, flags)
736cdef CUresult cuEventQuery(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
737 return cydriver._cuEventQuery(hEvent) 2xh?d@d{ ;iyh
739cdef CUresult cuEventSynchronize(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
740 return cydriver._cuEventSynchronize(hEvent) 21 { yhPc?i
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
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
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)
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)
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)
757cdef CUresult cuDestroyExternalMemory(CUexternalMemory extMem) except ?CUDA_ERROR_NOT_FOUND nogil:
758 return cydriver._cuDestroyExternalMemory(extMem)
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)
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)
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)
769cdef CUresult cuDestroyExternalSemaphore(CUexternalSemaphore extSem) except ?CUDA_ERROR_NOT_FOUND nogil:
770 return cydriver._cuDestroyExternalSemaphore(extSem)
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)
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)
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)
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)
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)
787cdef CUresult cuFuncGetAttribute(int* pi, CUfunction_attribute attrib, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil:
788 return cydriver._cuFuncGetAttribute(pi, attrib, hfunc)
790cdef CUresult cuFuncSetAttribute(CUfunction hfunc, CUfunction_attribute attrib, int value) except ?CUDA_ERROR_NOT_FOUND nogil:
791 return cydriver._cuFuncSetAttribute(hfunc, attrib, value)
793cdef CUresult cuFuncSetCacheConfig(CUfunction hfunc, CUfunc_cache config) except ?CUDA_ERROR_NOT_FOUND nogil:
794 return cydriver._cuFuncSetCacheConfig(hfunc, config)
796cdef CUresult cuFuncGetModule(CUmodule* hmod, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil:
797 return cydriver._cuFuncGetModule(hmod, hfunc)
799cdef CUresult cuFuncGetName(const char** name, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil:
800 return cydriver._cuFuncGetName(name, hfunc) 2j2
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)
805cdef CUresult cuFuncGetParamCount(CUfunction func, size_t* paramCount) except ?CUDA_ERROR_NOT_FOUND nogil:
806 return cydriver._cuFuncGetParamCount(func, paramCount)
808cdef CUresult cuFuncIsLoaded(CUfunctionLoadingState* state, CUfunction function) except ?CUDA_ERROR_NOT_FOUND nogil:
809 return cydriver._cuFuncIsLoaded(state, function)
811cdef CUresult cuFuncLoad(CUfunction function) except ?CUDA_ERROR_NOT_FOUND nogil:
812 return cydriver._cuFuncLoad(function)
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
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
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)
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)
826cdef CUresult cuLaunchHostFunc(CUstream hStream, CUhostFn fn, void* userData) except ?CUDA_ERROR_NOT_FOUND nogil:
827 return cydriver._cuLaunchHostFunc(hStream, fn, userData) 2LbMb
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)
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)
835cdef CUresult cuFuncSetSharedSize(CUfunction hfunc, unsigned int numbytes) except ?CUDA_ERROR_NOT_FOUND nogil:
836 return cydriver._cuFuncSetSharedSize(hfunc, numbytes)
838cdef CUresult cuParamSetSize(CUfunction hfunc, unsigned int numbytes) except ?CUDA_ERROR_NOT_FOUND nogil:
839 return cydriver._cuParamSetSize(hfunc, numbytes)
841cdef CUresult cuParamSeti(CUfunction hfunc, int offset, unsigned int value) except ?CUDA_ERROR_NOT_FOUND nogil:
842 return cydriver._cuParamSeti(hfunc, offset, value)
844cdef CUresult cuParamSetf(CUfunction hfunc, int offset, float value) except ?CUDA_ERROR_NOT_FOUND nogil:
845 return cydriver._cuParamSetf(hfunc, offset, value)
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)
850cdef CUresult cuLaunch(CUfunction f) except ?CUDA_ERROR_NOT_FOUND nogil:
851 return cydriver._cuLaunch(f)
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)
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)
859cdef CUresult cuParamSetTexRef(CUfunction hfunc, int texunit, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
860 return cydriver._cuParamSetTexRef(hfunc, texunit, hTexRef)
862cdef CUresult cuFuncSetSharedMemConfig(CUfunction hfunc, CUsharedconfig config) except ?CUDA_ERROR_NOT_FOUND nogil:
863 return cydriver._cuFuncSetSharedMemConfig(hfunc, config)
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
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
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
874cdef CUresult cuGraphKernelNodeSetParams(CUgraphNode hNode, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
875 return cydriver._cuGraphKernelNodeSetParams_v2(hNode, nodeParams)
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
880cdef CUresult cuGraphMemcpyNodeGetParams(CUgraphNode hNode, CUDA_MEMCPY3D* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
881 return cydriver._cuGraphMemcpyNodeGetParams(hNode, nodeParams) 1}
883cdef CUresult cuGraphMemcpyNodeSetParams(CUgraphNode hNode, const CUDA_MEMCPY3D* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
884 return cydriver._cuGraphMemcpyNodeSetParams(hNode, nodeParams)
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
889cdef CUresult cuGraphMemsetNodeGetParams(CUgraphNode hNode, CUDA_MEMSET_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
890 return cydriver._cuGraphMemsetNodeGetParams(hNode, nodeParams) 1b
892cdef CUresult cuGraphMemsetNodeSetParams(CUgraphNode hNode, const CUDA_MEMSET_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
893 return cydriver._cuGraphMemsetNodeSetParams(hNode, nodeParams)
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
898cdef CUresult cuGraphHostNodeGetParams(CUgraphNode hNode, CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
899 return cydriver._cuGraphHostNodeGetParams(hNode, nodeParams)
901cdef CUresult cuGraphHostNodeSetParams(CUgraphNode hNode, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
902 return cydriver._cuGraphHostNodeSetParams(hNode, nodeParams)
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
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
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
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
916cdef CUresult cuGraphEventRecordNodeGetEvent(CUgraphNode hNode, CUevent* event_out) except ?CUDA_ERROR_NOT_FOUND nogil:
917 return cydriver._cuGraphEventRecordNodeGetEvent(hNode, event_out)
919cdef CUresult cuGraphEventRecordNodeSetEvent(CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
920 return cydriver._cuGraphEventRecordNodeSetEvent(hNode, event)
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
925cdef CUresult cuGraphEventWaitNodeGetEvent(CUgraphNode hNode, CUevent* event_out) except ?CUDA_ERROR_NOT_FOUND nogil:
926 return cydriver._cuGraphEventWaitNodeGetEvent(hNode, event_out)
928cdef CUresult cuGraphEventWaitNodeSetEvent(CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
929 return cydriver._cuGraphEventWaitNodeSetEvent(hNode, event)
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)
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)
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)
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)
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)
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)
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)
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)
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)
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)
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
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
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
970cdef CUresult cuGraphMemFreeNodeGetParams(CUgraphNode hNode, CUdeviceptr* dptr_out) except ?CUDA_ERROR_NOT_FOUND nogil:
971 return cydriver._cuGraphMemFreeNodeGetParams(hNode, dptr_out)
973cdef CUresult cuDeviceGraphMemTrim(CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil:
974 return cydriver._cuDeviceGraphMemTrim(device) 1#$%
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
979cdef CUresult cuDeviceSetGraphMemAttribute(CUdevice device, CUgraphMem_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil:
980 return cydriver._cuDeviceSetGraphMemAttribute(device, attr, value) 1#$%
982cdef CUresult cuGraphClone(CUgraph* phGraphClone, CUgraph originalGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
983 return cydriver._cuGraphClone(phGraphClone, originalGraph) 2NbN _
985cdef CUresult cuGraphNodeFindInClone(CUgraphNode* phNode, CUgraphNode hOriginalNode, CUgraph hClonedGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
986 return cydriver._cuGraphNodeFindInClone(phNode, hOriginalNode, hClonedGraph)
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
991cdef CUresult cuGraphNodeGetContainingGraph(CUgraphNode hNode, CUgraph* phGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
992 return cydriver._cuGraphNodeGetContainingGraph(hNode, phGraph) 2*r
994cdef CUresult cuGraphNodeGetLocalId(CUgraphNode hNode, unsigned int* nodeId) except ?CUDA_ERROR_NOT_FOUND nogil:
995 return cydriver._cuGraphNodeGetLocalId(hNode, nodeId) 2@x
997cdef CUresult cuGraphNodeGetToolsId(CUgraphNode hNode, unsigned long long* toolsNodeId) except ?CUDA_ERROR_NOT_FOUND nogil:
998 return cydriver._cuGraphNodeGetToolsId(hNode, toolsNodeId) 2[x
1000cdef CUresult cuGraphGetId(CUgraph hGraph, unsigned int* graphId) except ?CUDA_ERROR_NOT_FOUND nogil:
1001 return cydriver._cuGraphGetId(hGraph, graphId) 2XL
1003cdef CUresult cuGraphExecGetId(CUgraphExec hGraphExec, unsigned int* graphId) except ?CUDA_ERROR_NOT_FOUND nogil:
1004 return cydriver._cuGraphExecGetId(hGraphExec, graphId) 2@i
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
1009cdef CUresult cuGraphGetRootNodes(CUgraph hGraph, CUgraphNode* rootNodes, size_t* numRootNodes) except ?CUDA_ERROR_NOT_FOUND nogil:
1010 return cydriver._cuGraphGetRootNodes(hGraph, rootNodes, numRootNodes)
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
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
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
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
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
1027cdef CUresult cuGraphDestroyNode(CUgraphNode hNode) except ?CUDA_ERROR_NOT_FOUND nogil:
1028 return cydriver._cuGraphDestroyNode(hNode) 2=xM B C =bYL
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
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
1036cdef CUresult cuGraphExecGetFlags(CUgraphExec hGraphExec, cuuint64_t* flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1037 return cydriver._cuGraphExecGetFlags(hGraphExec, flags)
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)
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)
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)
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)
1051cdef CUresult cuGraphExecChildGraphNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, CUgraph childGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1052 return cydriver._cuGraphExecChildGraphNodeSetParams(hGraphExec, hNode, childGraph)
1054cdef CUresult cuGraphExecEventRecordNodeSetEvent(CUgraphExec hGraphExec, CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1055 return cydriver._cuGraphExecEventRecordNodeSetEvent(hGraphExec, hNode, event)
1057cdef CUresult cuGraphExecEventWaitNodeSetEvent(CUgraphExec hGraphExec, CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1058 return cydriver._cuGraphExecEventWaitNodeSetEvent(hGraphExec, hNode, event)
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)
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)
1066cdef CUresult cuGraphNodeSetEnabled(CUgraphExec hGraphExec, CUgraphNode hNode, unsigned int isEnabled) except ?CUDA_ERROR_NOT_FOUND nogil:
1067 return cydriver._cuGraphNodeSetEnabled(hGraphExec, hNode, isEnabled)
1069cdef CUresult cuGraphNodeGetEnabled(CUgraphExec hGraphExec, CUgraphNode hNode, unsigned int* isEnabled) except ?CUDA_ERROR_NOT_FOUND nogil:
1070 return cydriver._cuGraphNodeGetEnabled(hGraphExec, hNode, isEnabled)
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# $ %
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}
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
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
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
1087cdef CUresult cuGraphKernelNodeCopyAttributes(CUgraphNode dst, CUgraphNode src) except ?CUDA_ERROR_NOT_FOUND nogil:
1088 return cydriver._cuGraphKernelNodeCopyAttributes(dst, src)
1090cdef CUresult cuGraphKernelNodeGetAttribute(CUgraphNode hNode, CUkernelNodeAttrID attr, CUkernelNodeAttrValue* value_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1091 return cydriver._cuGraphKernelNodeGetAttribute(hNode, attr, value_out)
1093cdef CUresult cuGraphKernelNodeSetAttribute(CUgraphNode hNode, CUkernelNodeAttrID attr, const CUkernelNodeAttrValue* value) except ?CUDA_ERROR_NOT_FOUND nogil:
1094 return cydriver._cuGraphKernelNodeSetAttribute(hNode, attr, value)
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
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
1102cdef CUresult cuUserObjectRetain(CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil:
1103 return cydriver._cuUserObjectRetain(object, count)
1105cdef CUresult cuUserObjectRelease(CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil:
1106 return cydriver._cuUserObjectRelease(object, count)
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
1111cdef CUresult cuGraphReleaseUserObject(CUgraph graph, CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil:
1112 return cydriver._cuGraphReleaseUserObject(graph, object, count)
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
1117cdef CUresult cuGraphNodeSetParams(CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1118 return cydriver._cuGraphNodeSetParams(hNode, nodeParams) 1}
1120cdef CUresult cuGraphNodeGetParams(CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1121 return cydriver._cuGraphNodeGetParams(hNode, nodeParams) 2-i
1123cdef CUresult cuGraphExecNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1124 return cydriver._cuGraphExecNodeSetParams(hGraphExec, hNode, nodeParams) 1}
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
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
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)
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
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)
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
1144cdef CUresult cuOccupancyMaxPotentialClusterSize(int* clusterSize, CUfunction func, const CUlaunchConfig* config) except ?CUDA_ERROR_NOT_FOUND nogil:
1145 return cydriver._cuOccupancyMaxPotentialClusterSize(clusterSize, func, config)
1147cdef CUresult cuOccupancyMaxActiveClusters(int* numClusters, CUfunction func, const CUlaunchConfig* config) except ?CUDA_ERROR_NOT_FOUND nogil:
1148 return cydriver._cuOccupancyMaxActiveClusters(numClusters, func, config)
1150cdef CUresult cuTexRefSetArray(CUtexref hTexRef, CUarray hArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1151 return cydriver._cuTexRefSetArray(hTexRef, hArray, Flags)
1153cdef CUresult cuTexRefSetMipmappedArray(CUtexref hTexRef, CUmipmappedArray hMipmappedArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1154 return cydriver._cuTexRefSetMipmappedArray(hTexRef, hMipmappedArray, Flags)
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)
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)
1162cdef CUresult cuTexRefSetFormat(CUtexref hTexRef, CUarray_format fmt, int NumPackedComponents) except ?CUDA_ERROR_NOT_FOUND nogil:
1163 return cydriver._cuTexRefSetFormat(hTexRef, fmt, NumPackedComponents)
1165cdef CUresult cuTexRefSetAddressMode(CUtexref hTexRef, int dim, CUaddress_mode am) except ?CUDA_ERROR_NOT_FOUND nogil:
1166 return cydriver._cuTexRefSetAddressMode(hTexRef, dim, am)
1168cdef CUresult cuTexRefSetFilterMode(CUtexref hTexRef, CUfilter_mode fm) except ?CUDA_ERROR_NOT_FOUND nogil:
1169 return cydriver._cuTexRefSetFilterMode(hTexRef, fm)
1171cdef CUresult cuTexRefSetMipmapFilterMode(CUtexref hTexRef, CUfilter_mode fm) except ?CUDA_ERROR_NOT_FOUND nogil:
1172 return cydriver._cuTexRefSetMipmapFilterMode(hTexRef, fm)
1174cdef CUresult cuTexRefSetMipmapLevelBias(CUtexref hTexRef, float bias) except ?CUDA_ERROR_NOT_FOUND nogil:
1175 return cydriver._cuTexRefSetMipmapLevelBias(hTexRef, bias)
1177cdef CUresult cuTexRefSetMipmapLevelClamp(CUtexref hTexRef, float minMipmapLevelClamp, float maxMipmapLevelClamp) except ?CUDA_ERROR_NOT_FOUND nogil:
1178 return cydriver._cuTexRefSetMipmapLevelClamp(hTexRef, minMipmapLevelClamp, maxMipmapLevelClamp)
1180cdef CUresult cuTexRefSetMaxAnisotropy(CUtexref hTexRef, unsigned int maxAniso) except ?CUDA_ERROR_NOT_FOUND nogil:
1181 return cydriver._cuTexRefSetMaxAnisotropy(hTexRef, maxAniso)
1183cdef CUresult cuTexRefSetBorderColor(CUtexref hTexRef, float* pBorderColor) except ?CUDA_ERROR_NOT_FOUND nogil:
1184 return cydriver._cuTexRefSetBorderColor(hTexRef, pBorderColor)
1186cdef CUresult cuTexRefSetFlags(CUtexref hTexRef, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1187 return cydriver._cuTexRefSetFlags(hTexRef, Flags)
1189cdef CUresult cuTexRefGetAddress(CUdeviceptr* pdptr, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1190 return cydriver._cuTexRefGetAddress_v2(pdptr, hTexRef)
1192cdef CUresult cuTexRefGetArray(CUarray* phArray, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1193 return cydriver._cuTexRefGetArray(phArray, hTexRef)
1195cdef CUresult cuTexRefGetMipmappedArray(CUmipmappedArray* phMipmappedArray, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1196 return cydriver._cuTexRefGetMipmappedArray(phMipmappedArray, hTexRef)
1198cdef CUresult cuTexRefGetAddressMode(CUaddress_mode* pam, CUtexref hTexRef, int dim) except ?CUDA_ERROR_NOT_FOUND nogil:
1199 return cydriver._cuTexRefGetAddressMode(pam, hTexRef, dim)
1201cdef CUresult cuTexRefGetFilterMode(CUfilter_mode* pfm, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1202 return cydriver._cuTexRefGetFilterMode(pfm, hTexRef)
1204cdef CUresult cuTexRefGetFormat(CUarray_format* pFormat, int* pNumChannels, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1205 return cydriver._cuTexRefGetFormat(pFormat, pNumChannels, hTexRef)
1207cdef CUresult cuTexRefGetMipmapFilterMode(CUfilter_mode* pfm, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1208 return cydriver._cuTexRefGetMipmapFilterMode(pfm, hTexRef)
1210cdef CUresult cuTexRefGetMipmapLevelBias(float* pbias, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1211 return cydriver._cuTexRefGetMipmapLevelBias(pbias, hTexRef)
1213cdef CUresult cuTexRefGetMipmapLevelClamp(float* pminMipmapLevelClamp, float* pmaxMipmapLevelClamp, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1214 return cydriver._cuTexRefGetMipmapLevelClamp(pminMipmapLevelClamp, pmaxMipmapLevelClamp, hTexRef)
1216cdef CUresult cuTexRefGetMaxAnisotropy(int* pmaxAniso, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1217 return cydriver._cuTexRefGetMaxAnisotropy(pmaxAniso, hTexRef)
1219cdef CUresult cuTexRefGetBorderColor(float* pBorderColor, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1220 return cydriver._cuTexRefGetBorderColor(pBorderColor, hTexRef)
1222cdef CUresult cuTexRefGetFlags(unsigned int* pFlags, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1223 return cydriver._cuTexRefGetFlags(pFlags, hTexRef)
1225cdef CUresult cuTexRefCreate(CUtexref* pTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1226 return cydriver._cuTexRefCreate(pTexRef)
1228cdef CUresult cuTexRefDestroy(CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1229 return cydriver._cuTexRefDestroy(hTexRef)
1231cdef CUresult cuSurfRefSetArray(CUsurfref hSurfRef, CUarray hArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1232 return cydriver._cuSurfRefSetArray(hSurfRef, hArray, Flags)
1234cdef CUresult cuSurfRefGetArray(CUarray* phArray, CUsurfref hSurfRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1235 return cydriver._cuSurfRefGetArray(phArray, hSurfRef)
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)
1240cdef CUresult cuTexObjectDestroy(CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1241 return cydriver._cuTexObjectDestroy(texObject)
1243cdef CUresult cuTexObjectGetResourceDesc(CUDA_RESOURCE_DESC* pResDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1244 return cydriver._cuTexObjectGetResourceDesc(pResDesc, texObject)
1246cdef CUresult cuTexObjectGetTextureDesc(CUDA_TEXTURE_DESC* pTexDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1247 return cydriver._cuTexObjectGetTextureDesc(pTexDesc, texObject)
1249cdef CUresult cuTexObjectGetResourceViewDesc(CUDA_RESOURCE_VIEW_DESC* pResViewDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1250 return cydriver._cuTexObjectGetResourceViewDesc(pResViewDesc, texObject)
1252cdef CUresult cuSurfObjectCreate(CUsurfObject* pSurfObject, const CUDA_RESOURCE_DESC* pResDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
1253 return cydriver._cuSurfObjectCreate(pSurfObject, pResDesc)
1255cdef CUresult cuSurfObjectDestroy(CUsurfObject surfObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1256 return cydriver._cuSurfObjectDestroy(surfObject)
1258cdef CUresult cuSurfObjectGetResourceDesc(CUDA_RESOURCE_DESC* pResDesc, CUsurfObject surfObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1259 return cydriver._cuSurfObjectGetResourceDesc(pResDesc, surfObject)
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)
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)
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)
1270cdef CUresult cuTensorMapReplaceAddress(CUtensorMap* tensorMap, void* globalAddress) except ?CUDA_ERROR_NOT_FOUND nogil:
1271 return cydriver._cuTensorMapReplaceAddress(tensorMap, globalAddress)
1273cdef CUresult cuDeviceCanAccessPeer(int* canAccessPeer, CUdevice dev, CUdevice peerDev) except ?CUDA_ERROR_NOT_FOUND nogil:
1274 return cydriver._cuDeviceCanAccessPeer(canAccessPeer, dev, peerDev)
1276cdef CUresult cuCtxEnablePeerAccess(CUcontext peerContext, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1277 return cydriver._cuCtxEnablePeerAccess(peerContext, Flags)
1279cdef CUresult cuCtxDisablePeerAccess(CUcontext peerContext) except ?CUDA_ERROR_NOT_FOUND nogil:
1280 return cydriver._cuCtxDisablePeerAccess(peerContext)
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)
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)
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
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)
1294cdef CUresult cuGraphicsResourceGetMappedMipmappedArray(CUmipmappedArray* pMipmappedArray, CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil:
1295 return cydriver._cuGraphicsResourceGetMappedMipmappedArray(pMipmappedArray, resource)
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
1300cdef CUresult cuGraphicsResourceSetMapFlags(CUgraphicsResource resource, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1301 return cydriver._cuGraphicsResourceSetMapFlags_v2(resource, flags)
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
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
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)
1312cdef CUresult cuCoredumpGetAttribute(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil:
1313 return cydriver._cuCoredumpGetAttribute(attrib, value, size)
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
1318cdef CUresult cuCoredumpSetAttribute(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil:
1319 return cydriver._cuCoredumpSetAttribute(attrib, value, size)
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
1324cdef CUresult cuCoredumpRegisterStartCallback(CUcoredumpStatusCallback callback, void* userData, CUcoredumpCallbackHandle* callbackOut) except ?CUDA_ERROR_NOT_FOUND nogil:
1325 return cydriver._cuCoredumpRegisterStartCallback(callback, userData, callbackOut)
1327cdef CUresult cuCoredumpRegisterCompleteCallback(CUcoredumpStatusCallback callback, void* userData, CUcoredumpCallbackHandle* callbackOut) except ?CUDA_ERROR_NOT_FOUND nogil:
1328 return cydriver._cuCoredumpRegisterCompleteCallback(callback, userData, callbackOut)
1330cdef CUresult cuCoredumpDeregisterStartCallback(CUcoredumpCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil:
1331 return cydriver._cuCoredumpDeregisterStartCallback(callback)
1333cdef CUresult cuCoredumpDeregisterCompleteCallback(CUcoredumpCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil:
1334 return cydriver._cuCoredumpDeregisterCompleteCallback(callback)
1336cdef CUresult cuGetExportTable(const void** ppExportTable, const CUuuid* pExportTableId) except ?CUDA_ERROR_NOT_FOUND nogil:
1337 return cydriver._cuGetExportTable(ppExportTable, pExportTableId)
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
1342cdef CUresult cuGreenCtxDestroy(CUgreenCtx hCtx) except ?CUDA_ERROR_NOT_FOUND nogil:
1343 return cydriver._cuGreenCtxDestroy(hCtx) 2~kGEHEIEV W JEKELEMENEOE
1345cdef CUresult cuCtxFromGreenCtx(CUcontext* pContext, CUgreenCtx hCtx) except ?CUDA_ERROR_NOT_FOUND nogil:
1346 return cydriver._cuCtxFromGreenCtx(pContext, hCtx) 2~kujvjueV W wjxjyjzjAjBj
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
1351cdef CUresult cuCtxGetDevResource(CUcontext hCtx, CUdevResource* resource, CUdevResourceType typename) except ?CUDA_ERROR_NOT_FOUND nogil:
1352 return cydriver._cuCtxGetDevResource(hCtx, resource, typename)
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
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
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
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
1366cdef CUresult cuGreenCtxRecordEvent(CUgreenCtx hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
1367 return cydriver._cuGreenCtxRecordEvent(hCtx, hEvent)
1369cdef CUresult cuGreenCtxWaitEvent(CUgreenCtx hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
1370 return cydriver._cuGreenCtxWaitEvent(hCtx, hEvent)
1372cdef CUresult cuStreamGetGreenCtx(CUstream hStream, CUgreenCtx* phCtx) except ?CUDA_ERROR_NOT_FOUND nogil:
1373 return cydriver._cuStreamGetGreenCtx(hStream, phCtx)
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
1378cdef CUresult cuGreenCtxGetId(CUgreenCtx greenCtx, unsigned long long* greenCtxId) except ?CUDA_ERROR_NOT_FOUND nogil:
1379 return cydriver._cuGreenCtxGetId(greenCtx, greenCtxId)
1381cdef CUresult cuStreamGetDevResource(CUstream hStream, CUdevResource* resource, CUdevResourceType typename) except ?CUDA_ERROR_NOT_FOUND nogil:
1382 return cydriver._cuStreamGetDevResource(hStream, resource, typename) 2UL
1384cdef CUresult cuLogsRegisterCallback(CUlogsCallback callbackFunc, void* userData, CUlogsCallbackHandle* callback_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1385 return cydriver._cuLogsRegisterCallback(callbackFunc, userData, callback_out)
1387cdef CUresult cuLogsUnregisterCallback(CUlogsCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil:
1388 return cydriver._cuLogsUnregisterCallback(callback)
1390cdef CUresult cuLogsCurrent(CUlogIterator* iterator_out, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1391 return cydriver._cuLogsCurrent(iterator_out, flags)
1393cdef CUresult cuLogsDumpToFile(CUlogIterator* iterator, const char* pathToFile, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1394 return cydriver._cuLogsDumpToFile(iterator, pathToFile, flags)
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)
1399cdef CUresult cuCheckpointProcessGetRestoreThreadId(int pid, int* tid) except ?CUDA_ERROR_NOT_FOUND nogil:
1400 return cydriver._cuCheckpointProcessGetRestoreThreadId(pid, tid)
1402cdef CUresult cuCheckpointProcessGetState(int pid, CUprocessState* state) except ?CUDA_ERROR_NOT_FOUND nogil:
1403 return cydriver._cuCheckpointProcessGetState(pid, state) 2a3
1405cdef CUresult cuCheckpointProcessLock(int pid, CUcheckpointLockArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil:
1406 return cydriver._cuCheckpointProcessLock(pid, args)
1408cdef CUresult cuCheckpointProcessCheckpoint(int pid, CUcheckpointCheckpointArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil:
1409 return cydriver._cuCheckpointProcessCheckpoint(pid, args)
1411cdef CUresult cuCheckpointProcessRestore(int pid, CUcheckpointRestoreArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil:
1412 return cydriver._cuCheckpointProcessRestore(pid, args)
1414cdef CUresult cuCheckpointProcessUnlock(int pid, CUcheckpointUnlockArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil:
1415 return cydriver._cuCheckpointProcessUnlock(pid, args)
1417cdef CUresult cuProfilerStart() except ?CUDA_ERROR_NOT_FOUND nogil:
1418 return cydriver._cuProfilerStart() 2'Y
1420cdef CUresult cuProfilerStop() except ?CUDA_ERROR_NOT_FOUND nogil:
1421 return cydriver._cuProfilerStop() 2'Y
1423cdef CUresult cuGraphicsEGLRegisterImage(CUgraphicsResource* pCudaResource, EGLImageKHR image, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1424 return cydriver._cuGraphicsEGLRegisterImage(pCudaResource, image, flags)
1426cdef CUresult cuEGLStreamConsumerConnect(CUeglStreamConnection* conn, EGLStreamKHR stream) except ?CUDA_ERROR_NOT_FOUND nogil:
1427 return cydriver._cuEGLStreamConsumerConnect(conn, stream)
1429cdef CUresult cuEGLStreamConsumerConnectWithFlags(CUeglStreamConnection* conn, EGLStreamKHR stream, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1430 return cydriver._cuEGLStreamConsumerConnectWithFlags(conn, stream, flags)
1432cdef CUresult cuEGLStreamConsumerDisconnect(CUeglStreamConnection* conn) except ?CUDA_ERROR_NOT_FOUND nogil:
1433 return cydriver._cuEGLStreamConsumerDisconnect(conn)
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)
1438cdef CUresult cuEGLStreamConsumerReleaseFrame(CUeglStreamConnection* conn, CUgraphicsResource pCudaResource, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1439 return cydriver._cuEGLStreamConsumerReleaseFrame(conn, pCudaResource, pStream)
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)
1444cdef CUresult cuEGLStreamProducerDisconnect(CUeglStreamConnection* conn) except ?CUDA_ERROR_NOT_FOUND nogil:
1445 return cydriver._cuEGLStreamProducerDisconnect(conn)
1447cdef CUresult cuEGLStreamProducerPresentFrame(CUeglStreamConnection* conn, CUeglFrame eglframe, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1448 return cydriver._cuEGLStreamProducerPresentFrame(conn, eglframe, pStream)
1450cdef CUresult cuEGLStreamProducerReturnFrame(CUeglStreamConnection* conn, CUeglFrame* eglframe, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1451 return cydriver._cuEGLStreamProducerReturnFrame(conn, eglframe, pStream)
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)
1456cdef CUresult cuEventCreateFromEGLSync(CUevent* phEvent, EGLSyncKHR eglSync, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1457 return cydriver._cuEventCreateFromEGLSync(phEvent, eglSync, flags)
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
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
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)
1468cdef CUresult cuVDPAUGetDevice(CUdevice* pDevice, VdpDevice vdpDevice, VdpGetProcAddress* vdpGetProcAddress) except ?CUDA_ERROR_NOT_FOUND nogil:
1469 return cydriver._cuVDPAUGetDevice(pDevice, vdpDevice, vdpGetProcAddress)
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)
1474cdef CUresult cuGraphicsVDPAURegisterVideoSurface(CUgraphicsResource* pCudaResource, VdpVideoSurface vdpSurface, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1475 return cydriver._cuGraphicsVDPAURegisterVideoSurface(pCudaResource, vdpSurface, flags)
1477cdef CUresult cuGraphicsVDPAURegisterOutputSurface(CUgraphicsResource* pCudaResource, VdpOutputSurface vdpSurface, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1478 return cydriver._cuGraphicsVDPAURegisterOutputSurface(pCudaResource, vdpSurface, flags)