B \@sdZddlmZmZmZddlZddlZddlmZddl m Z Gddde Z Gd d d e Z Gd d d e Z e ZejZdd dZddZddZdS)a Expose each GPU devices directly. This module implements a API that is like the "CUDA runtime" context manager for managing CUDA context stack and clean up. It relies on thread-local globals to separate the context stack management of each thread. Contexts are also sharable among threads. Only the main thread can destroy Contexts. Note: - This module must be imported by the main-thread. )print_functionabsolute_importdivisionN) servicelib)drivercsHeZdZfddZddZddZddZd d Zed d Z Z S) _DeviceListcs<|dkr,t}ddt|D}||_|Stt||S)NlstcSsg|]}tt|qS)_DeviceContextManagerrZ get_device).0Zdevidr r 9lib/python3.7/site-packages/numba/cuda/cudadrv/devices.py sz+_DeviceList.__getattr__..)rZget_device_countranger superr __getattr__)selfattrZnumdevgpus) __class__r r rs z_DeviceList.__getattr__cCs |j|S)zB Returns the context manager for device *devnum*. )r )rdevnumr r r __getitem__$sz_DeviceList.__getitem__cCsddd|jDS)Nz, cSsg|] }t|qSr )str)r dr r r r+sz'_DeviceList.__str__..)joinr )rr r r __str__*sz_DeviceList.__str__cCs t|jS)N)iterr )rr r r __iter__-sz_DeviceList.__iter__cCs t|jS)N)lenr )rr r r __len__0sz_DeviceList.__len__cCstjr|jtjjjSdS)zFReturns the active device or None if there's no active device N)_runtime context_stackr current_contextdeviceid)rr r r current3sz_DeviceList.current) __name__ __module__ __qualname__rrrrrpropertyr% __classcell__r r )rr rs  rc@s8eZdZdZddZddZddZdd Zd d Zd S) r aU Provides a context manager for executing in the context of the chosen device. The normal use of instances of this type is from ``numba.cuda.gpus``. For example, to execute on device 2:: with numba.cuda.gpus[2]: d_a = numba.cuda.to_device(a) to copy the array *a* onto device 2, referred to by *d_a*. cCs ||_dS)N)_device)rr#r r r __init__Gsz_DeviceContextManager.__init__cCs t|j|S)N)getattrr+)ritemr r r rJsz!_DeviceContextManager.__getattr__cCst|dS)N)r push_context)rr r r __enter__Msz_DeviceContextManager.__enter__cCs tdS)N)r pop_context)rexc_typeZexc_valZexc_tbr r r __exit__Psz_DeviceContextManager.__exit__cCs dj|dS)Nz)r)format)rr r r rSsz_DeviceContextManager.__str__N) r&r'r(__doc__r,rr0r3rr r r r r ;s  r c@sTeZdZdZddZeddZddZdd Zd d Z d d Z ddZ ddZ dS)_RuntimezEmulate the CUDA runtime context management. It owns all Devices and Contexts. Keeps at most one Context per Device cCs*t|_t|_t|_t|_ dS)N) rrrZTLStackr! threadingcurrent_thread _mainthreadRLock_lock)rr r r r,^s  z_Runtime.__init__cCs|jjS)z&Return the active gpu context )r!top)rr r r r"ksz_Runtime.current_contextc Cs&|j|}||SQRXdS)zTry to use a already created context for the given gpu. If none existed, create a new context. Returns the context N)r;Zget_primary_contextpush)rgpuctxr r r _get_or_create_contextqsz_Runtime._get_or_create_contextcCs6|jjs|jj|kr ||}n|j}|j||S)zlPush a context for the given GPU or create a new one if no context exist for the given GPU. )r!Zis_emptyr"r#r@r=)rr>r?r r r r/|s   z_Runtime.push_contextcCs4|j}t|jdkr&||j|js0tdS)zPop a context from the context stack if there is more than one context in the stack. Will not remove the last context in the stack. rN)r"rr!popAssertionError)rr?r r r r1s  z_Runtime.pop_contextc Cs.|jr |jS|j||j|SQRXdS)zoReturns the current context or push/create a context for the GPU with the given device number. N)r!r"r;r/r)rrr r r get_or_create_contextsz_Runtime.get_or_create_contextcCs8x|jr|j}|qWt|jkr4|dS)zqClear all contexts in the thread. Destroy the context if and only if we are in the main thread. N)r!rAr7r8r9_destroy_all_contexts)rr?r r r resets   z_Runtime.resetcCsx|jD] }|qWdS)N)rrE)rr>r r r rDs z_Runtime._destroy_all_contextsN) r&r'r(r5r,r)r"r@r/r1rCrErDr r r r r6Ws    r6cCs t|S)z^Get the current device or use a device by device number, and return the CUDA context. )r rC)rr r r get_contextsrFcstfdd}|S)z A decorator that ensures a CUDA context is available when *fn* is executed. Decorating *fn* is equivalent to writing:: get_context() fn() at each call site. cst||S)N)rF)argsZkws)fnr r _require_cuda_contextsz.require_context.._require_cuda_context) functoolswraps)rHrIr )rHr require_contexts rLcCs tdS)zReset the CUDA subsystem for the current thread. In the main thread: This removes all CUDA contexts. Only use this at shutdown or for cleaning up between tests. In non-main threads: This clear the CUDA context stack only. N)r rEr r r r rEs rE)r)r5Z __future__rrrrJr7Znumbarrobjectrr r6r rrFrLrEr r r r  s  '`