σ
\K]c           @` s<  d  d l  m Z m Z m Z d  d l Z d  d l Z d d l m Z d d l m Z d d l	 m
 Z
 m Z e j Z e j Z e j Z d e j f d	     YZ e j Z e j Z e j Z e j Z e j Z e j Z e Z e j Z e j Z e j Z e j Z e j Z e Z  e j! re j n e j" Z# e j Z$ e j Z% e Z& e j Z' e j Z( d
 e j f d     YZ) e j Z* e j Z+ e j Z, e j Z- e j Z. e j Z/ d e j f d     YZ0 d e j f d     YZ1 d e j f d     YZ2 e2 Z3 e j Z4 e j Z5 e j Z6 e j Z7 e j Z8 e j Z9 e j Z: e Z; e j Z< e Z= e Z> e j Z? e j Z@ e ZA e j ZB e ZC e j ZD e j ZE e ZF e j ZG e j" ZH d ZI d e j f d     YZJ e eJ  ZK e j ZL e j ZM e j ZN d e j f d     YZO e e jP e jQ e# e jR   ZS e j ZT e ZU e j ZV e j ZW e j ZX e j ZY e j ZZ e j Z[ d e j f d     YZ\ eK Z] e Z^ e j Z_ e j Z` d e j f d     YZa e jP e e e e e jb e e^   Zc e jP e e^  Zd e jP e e^ e]  Ze e jP e e^ e] e jR  Zf e jP e e^ ef e jR  Zg e jP e e^ e_ e jR  Zh e jP e e^ e; e ji ea e jb e? e e=   Zj d e j f d     YZk e Zl e j Zm e j Zn e j Zo d e j f d     YZp d e j f d      YZq e j Zr d! e j f d"     YZs d# e j f d$     YZt e Zu e j Zv e j Zw e j Zx d% e j f d&     YZy e jP e e e jz  Z{ e jP d e e e)  e jz  Z} e jP e e& e jz  Z~ e jP e e= eA e jz  Z e jP e e j e> e e jR   Z e jP d e jR  Z e jP e eU e jR  Z d'   Z e   \ Z Z d(   Z iy i e d) 6e e e jb  g d* 6e d+ 6d, 6i e d) 6g  d* 6e d+ 6d- 6i e d) 6g  d* 6e d+ 6d. 6i e d) 6e e jR g d* 6e d+ 6d/ 6i e d) 6e j e j e j e e jQ  g d* 6e d+ 6d0 6i e d) 6e j e j e j e jR g d* 6e d+ 6d1 6i e d) 6e e e jR g d* 6e d+ 6d2 6i e d) 6e{ e jz g d* 6e d+ 6d3 6i e d) 6e e e e j  g d* 6e d+ 6d4 6i e d) 6e j e e j e j e e jQ  g d* 6e d+ 6d5 6i e d) 6e# e j" e e  e e   g d* 6e d+ 6d6 6i e d) 6e  g d* 6e d+ 6d7 6i e# d) 6e  g d* 6d8 6i e# d) 6e  g d* 6d9 6i d d) 6e  e# g d* 6d: 6i d d) 6e  e# g d* 6d; 6i e# d) 6e  e# g d* 6d< 6i e# d) 6e  e# g d* 6d= 6i e# d) 6e  e# g d* 6d> 6i e# d) 6e  e# g d* 6d? 6i e# d) 6e  e# e# g d* 6d@ 6i e# d) 6e  e# e# g d* 6dA 6i e# d) 6e  e# e# g d* 6dB 6i e# d) 6e  e# e# g d* 6dC 6i d d) 6e  e# g d* 6dD 6i d d) 6e  e# g d* 6dE 6i d d) 6e  e# g d* 6dF 6i d d) 6e  e# g d* 6dG 6i d d) 6e  e# g d* 6dH 6i d d) 6e  e# g d* 6dI 6i d d) 6e  e# g d* 6dJ 6i d d) 6e  e# g d* 6dK 6i d d) 6e  e# g d* 6dL 6i d d) 6e  e# g d* 6dM 6i d d) 6e  e# g d* 6dN 6i d d) 6e  e# g d* 6dO 6i d d) 6e  e# g d* 6dP 6i d d) 6e  e# g d* 6dQ 6i d d) 6e  e# g d* 6dR 6i d d) 6e  e# g d* 6dS 6i d d) 6e  e# g d* 6dT 6i d d) 6e  e# g d* 6dU 6i d d) 6e  e# g d* 6dV 6i d d) 6e  e# g d* 6dW 6i e# d) 6e  e$ e# e j e% g d* 6dX 6i e# d) 6e  e$ e# e j e% g d* 6dY 6i e d) 6e e j" e' e} e jR e j" e j" e e e)   g d* 6e d+ 6dZ 6i e d) 6e& e j" e' e j" e  e e e)   g d* 6e d+ 6d[ 6i e d) 6e e)  g d* 6e d+ 6d\ 6i e d) 6e e)  g d* 6e d+ 6d] 6i e j d) 6e e)  g d* 6d^ 6i e j d) 6e e)  g d* 6d_ 6i e j d) 6e e)  g d* 6d` 6i e j d) 6e e)  g d* 6da 6i d d) 6e e)  e j g d* 6db 6i d d) 6e e)  e j g d* 6dc 6i e j d) 6e e)  e j e j g d* 6dd 6i e j d) 6e e)  e j e j g d* 6de 6i e j d) 6e e)  e j e j g d* 6df 6i e j d) 6e e)  e j e j g d* 6dg 6i e j d) 6e e)  e j g d* 6dh 6i e j d) 6e e)  e j g d* 6di 6i e j d) 6e e)  e j g d* 6dj 6i e j d) 6e e)  e j g d* 6dk 6i d d) 6e e)  e j g d* 6dl 6i d d) 6e e)  e j g d* 6dm 6i e d) 6e& e6 e jR g d* 6e d+ 6dn 6i e d) 6e e~ e jz g d* 6e d+ 6do 6i e d) 6e& e j e e jR  g d* 6e d+ 6dp 6i e d) 6e jR g d* 6e d+ 6dq 6i e d) 6e jR e jR e j g d* 6e d+ 6dr 6i e d) 6e jR e e g d* 6e d+ 6ds 6i e d) 6e jR e j g d* 6e d+ 6dt 6i e d) 6e jR e j g d* 6e d+ 6du 6i e d) 6e jb e e;  g d* 6e d+ 6dv 6i e d) 6e; e< e jR g d* 6e d+ 6dw 6i e d) 6e; e; e e jQ  g d* 6e d+ 6dx 6i e d) 6e e> e e jR  e> e jb e e jR  e e j  g d* 6e d+ 6dy 6i e d) 6e jR e j e jb e e=  g d* 6e d+ 6dz 6i e d) 6e= g d* 6e d+ 6d{ 6i e d) 6e= e@ e jR g d* 6e d+ 6d| 6i e d) 6e= e jb e eA  g d* 6e d+ 6d} 6i e d) 6eA eB e jR g d* 6e d+ 6d~ 6i e d) 6e= e e jR g d* 6e d+ 6d 6i e d) 6e eD e jb e j eC  g d* 6e d+ 6d 6i e d+ 6e d) 6eC g d* 6d 6i e d+ 6e d) 6eC e e= e jb g d* 6d 6i e d+ 6e d) 6eC e jb g d* 6d 6i e d+ 6e d) 6eC eE e jR g d* 6d 6i e d) 6eC e jb e jR g d* 6e d+ 6d 6i e d) 6eC e e jb e jR g d* 6e d+ 6d 6i e d) 6eC e e jb e jR g d* 6e d+ 6d 6i e d) 6eC e e j"  g d* 6e d+ 6d 6i e d+ 6e d) 6eC e jb e jb e e ji e j eF  g d* 6d 6i e d+ 6e d) 6eF eG e jR g d* 6d 6i e d+ 6e d) 6eF eG e jR g d* 6d 6i e d+ 6e d) 6e e eN  g d* 6d 6i e d+ 6e d) 6e eN g d* 6d 6i e d+ 6e d) 6e e)  e j g d* 6d 6i e d+ 6e d) 6e e  e eO  g d* 6d 6i e d+ 6e d) 6e j e e j  g d* 6d 6i e d+ 6e d) 6e  e$ e# eS e jR g d* 6d 6i e d+ 6e d) 6e j e  e jR g d* 6d 6i e d+ 6e j" d) 6e j" e e   e e$  e e#  e j e% e e#  g d* 6d 6i e d+ 6e d) 6e e e jR g d* 6d 6i e d+ 6e d) 6e e)  e j" e e j"  g d* 6d 6i e d+ 6e d) 6eU eW e jR g d* 6d 6i e d+ 6e d) 6e e e jR g d* 6d 6i e d+ 6e d) 6eU e j e j" e e jR  g d* 6d 6i e d+ 6e d) 6e jR g d* 6d 6i e d+ 6e d) 6e jR e e jR e e j e j" e e   e  g d* 6d 6i e d+ 6e d) 6e eU e[ e jR g d* 6d 6i e d+ 6e d) 6e j" e e  e e j"  e jR g d* 6d 6i e d+ 6e d) 6eU eU e e jQ  g d* 6d 6i e d+ 6e d) 6e jR eU e j" g d* 6d 6i e d+ 6e d) 6e jR e j e e  e j e e jR  g d* 6d 6i e d+ 6e d) 6e jR g d* 6d 6i e d+ 6e d) 6e jR g d* 6d 6i e d+ 6e d) 6e j" e e  e j e j" e e j  e e jR  e e j  e e jR  g d* 6d  6i e d+ 6e d) 6e e jR  g d* 6d  6i e d+ 6e d) 6e e eq  e e\  e jR e el g d* 6d‘ 6Z d S(’   i    (   t   print_functiont   absolute_importt   divisionNi   (   t   utilsi   (   t   enums(   t   HsaApiErrort
   HsaWarningt
   hsa_dim3_tc           B` s2   e  Z d  e j f d e j f d e j f g Z RS(   t   xt   yt   z(   t   __name__t
   __module__t   ctypest   c_uint32t   _fields_(    (    (    s6   lib/python2.7/site-packages/numba/roc/hsadrv/drvapi.pyR      s   t   hsa_queue_tc           B` sb   e  Z d  Z d e f d e j f d e j f d e f d e j f d e j f d e j f g Z RS(   sw   In theory, this should be aligned to 64 bytes. In any case, allocation
    of this structure is done by the hsa libraryt   typet   featurest   base_addresst   doorbell_signalt   sizet	   reserved1t   id(	   R   R   t   __doc__t   hsa_queue_type_tR   R   t   c_void_pt   hsa_signal_tR   (    (    (    s6   lib/python2.7/site-packages/numba/roc/hsadrv/drvapi.pyR   .   s   		t   hsa_kernel_dispatch_packet_tc           B` sΏ   e  Z d  e j f d e j f d e j f d e j f d e j f d e j f d e j f d e j f d e j f d	 e j f d
 e j f d e j f d e j f d e j f d e f g Z RS(   t   headert   setupt   workgroup_size_xt   workgroup_size_yt   workgroup_size_zt	   reserved0t   grid_size_xt   grid_size_yt   grid_size_zt   private_segment_sizet   group_segment_sizet   kernel_objectt   kernarg_addresst	   reserved2t   completion_signal(   R   R   R   t   c_uint16R   t   c_uint64R   R   (    (    (    s6   lib/python2.7/site-packages/numba/roc/hsadrv/drvapi.pyR   @   s   t   hsa_agent_dispatch_packet_tc           B` si   e  Z d  Z d e j f d e j f d e j f d e j f d e j d f d e j f d e f g Z	 RS(	   s5   This should be aligned to HSA_PACKET_ALIGN_BYTES (64)R   R   R"   t   return_addresst   argi   R*   R+   (
   R   R   R   R   R,   R   R   R-   R   R   (    (    (    s6   lib/python2.7/site-packages/numba/roc/hsadrv/drvapi.pyR.   U   s   t   hsa_barrier_and_packet_tc           B` st   e  Z d  e j f d e j f d e j f d e f d e f d e f d e f d e f d e j f d	 e f g
 Z RS(
   R   R"   R   t   dep_signal0t   dep_signal1t   dep_signal2t   dep_signal3t   dep_signal4R*   R+   (   R   R   R   R,   R   R   R-   R   (    (    (    s6   lib/python2.7/site-packages/numba/roc/hsadrv/drvapi.pyR1   a   s   					i   t   BrigModuleHeaderc        	   B` sp   e  Z d  e j e f d e f d e f d e j f d e j d f d e j f d e j f d e j f g Z	 RS(	   t   identificationt	   brigMajort	   brigMinort	   byteCountt   hashi@   t   reservedt   sectionCountt   sectionIndex(
   R   R   R   t   c_chart   MODULE_IDENTIFICATION_LENGTHt   BrigVersion32_tR-   t   c_uint8R   R   (    (    (    s6   lib/python2.7/site-packages/numba/roc/hsadrv/drvapi.pyR7      s   		t!   hsa_amd_profiling_dispatch_time_tc           B` s&   e  Z d  e j f d e j f g Z RS(   t   startt   end(   R   R   R   R-   R   (    (    (    s6   lib/python2.7/site-packages/numba/roc/hsadrv/drvapi.pyRD   £   s   t   hsa_amd_image_descriptor_tc           B` s6   e  Z d  e j f d e j f d e j d f g Z RS(   t   versiont   deviceIDt   datai   (   R   R   R   R   R   (    (    (    s6   lib/python2.7/site-packages/numba/roc/hsadrv/drvapi.pyRG   Έ   s   t   hsa_ext_control_directives_tc           B` s   e  Z d  e j f d e j f d e j f d e j f d e j f d e j f d e j f d e j d f d	 e f d
 e j f d e j d f g Z RS(   t   control_directives_maskt   break_exceptions_maskt   detect_exceptions_maskt   max_dynamic_group_sizet   max_flat_grid_sizet   max_flat_workgroup_sizeR   t   required_grid_sizei   t   required_workgroup_sizet   required_dimR*   iK   (	   R   R   R   R-   R,   R   R   RC   R   (    (    (    s6   lib/python2.7/site-packages/numba/roc/hsadrv/drvapi.pyRK   Θ   s   	t   hsa_ext_finalizer_1_00_pfn_tc           B` sD   e  Z d  e f d e f d e f d e f d e f d e f g Z RS(   t   hsa_ext_program_createt   hsa_ext_program_destroyt   hsa_ext_program_add_modulet   hsa_ext_program_iterate_modulest   hsa_ext_program_get_infot   hsa_ext_program_finalize(	   R   R   t   HSA_EXT_PROGRAM_CREATE_FPTRt   HSA_EXT_PROGRAM_DESTROY_FPTRt   HSA_EXT_PROGRAM_ADD_MODULE_FPTRt$   HSA_EXT_PROGRAM_ITERATE_MODULES_FPTRt   HSA_EXT_PROGRAM_GET_INFO_FPTRt   HSA_EXT_PROGRAM_FINALIZE_FPTRR   (    (    (    s6   lib/python2.7/site-packages/numba/roc/hsadrv/drvapi.pyRU     s   				t   hsa_ext_image_format_tc           B` s    e  Z d  e f d e f g Z RS(   t   channel_typet   channel_order(   R   R   t   hsa_ext_image_channel_type_tt   hsa_ext_image_channel_order_tR   (    (    (    s6   lib/python2.7/site-packages/numba/roc/hsadrv/drvapi.pyRb     s   	t   hsa_ext_image_descriptor_tc           B` sP   e  Z d  e f d e j f d e j f d e j f d e j f d e f g Z RS(   t   geometryt   widtht   heightt   deptht
   array_sizet   format(   R   R   t   hsa_ext_image_geometry_tR   t   c_size_tRb   R   (    (    (    s6   lib/python2.7/site-packages/numba/roc/hsadrv/drvapi.pyRg   $  s   	t   hsa_ext_image_data_info_tc           B` s&   e  Z d  e j f d e j f g Z RS(   R   t	   alignment(   R   R   R   Ro   R   (    (    (    s6   lib/python2.7/site-packages/numba/roc/hsadrv/drvapi.pyRp   0  s   t   hsa_ext_image_region_tc           B` s    e  Z d  e f d  e f g Z RS(   t   offset(   R   R   R   R   (    (    (    s6   lib/python2.7/site-packages/numba/roc/hsadrv/drvapi.pyRr   6  s   	t   hsa_ext_sampler_descriptor_tc           B` s)   e  Z d  e f d e f d e f g Z RS(   t   coordinate_modet   filter_modet   address_mode(   R   R   t!   hsa_ext_sampler_coordinate_mode_tt   hsa_ext_sampler_filter_mode_tt!   hsa_ext_sampler_addressing_mode_tR   (    (    (    s6   lib/python2.7/site-packages/numba/roc/hsadrv/drvapi.pyRt   A  s   		c          C` s   t  j   }  t  j   } xw g  t t  D] } | j d  r( | ^ q( D]G } t t |  } d | k ru | |  | <qG d | k rG | | | <qG qG W|  | f S(   Nt   HSA_t   STATUS_ERRORt   STATUS_INFO(   R   t
   UniqueDictt   dirR   t
   startswitht   getattr(   t   err_mapt   warn_mapt   namet   code(    (    s6   lib/python2.7/site-packages/numba/roc/hsadrv/drvapi.pyt   _build_reverse_error_warn_maps|  s    5c         C` s   |  t  j k r |  t  j k rW t j |  d  } d j | j |  } t |  |   q t j |  d  } d j | j |  } t	 j
 | t  n  d  S(   Nt   UNKNOWN_HSA_ERRORs   Call to {0} returned {1}t   UNKNOWN_HSA_INFO(   R   t   HSA_STATUS_SUCCESSt   HSA_STATUS_ERRORt	   ERROR_MAPt   getRm   R   R   t   WARN_MAPt   warningst   warnR   (   t   resultt   funct	   argumentst   errnamet   msgt   warnname(    (    s6   lib/python2.7/site-packages/numba/roc/hsadrv/drvapi.pyt   _check_error  s    t   restypet   argtypest   errcheckt   hsa_status_stringt   hsa_initt   hsa_shut_downt   hsa_system_get_infot   hsa_system_extension_supportedt   hsa_system_get_extension_tablet   hsa_agent_get_infot   hsa_iterate_agentst    hsa_agent_get_exception_policiest   hsa_agent_extension_supportedt   hsa_signal_createt   hsa_signal_destroyt   hsa_signal_load_acquiret   hsa_signal_load_relaxedt   hsa_signal_store_relaxedt   hsa_signal_store_releaset   hsa_signal_exchange_acq_relt   hsa_signal_exchange_acquiret   hsa_signal_exchange_relaxedt   hsa_signal_exchange_releaset   hsa_signal_cas_acq_relt   hsa_signal_cas_acquiret   hsa_signal_cas_relaxedt   hsa_signal_cas_releaset   hsa_signal_add_acq_relt   hsa_signal_add_acquiret   hsa_signal_add_relaxedt   hsa_signal_add_releaset   hsa_signal_subtract_acq_relt   hsa_signal_subtract_acquiret   hsa_signal_subtract_relaxedt   hsa_signal_subtract_releaset   hsa_signal_and_acq_relt   hsa_signal_and_acquiret   hsa_signal_and_relaxedt   hsa_signal_and_releaset   hsa_signal_or_acq_relt   hsa_signal_or_acquiret   hsa_signal_or_relaxedt   hsa_signal_or_releaset   hsa_signal_xor_acq_relt   hsa_signal_xor_acquiret   hsa_signal_xor_relaxedt   hsa_signal_xor_releaset   hsa_signal_wait_acquiret   hsa_signal_wait_relaxedt   hsa_queue_createt   hsa_soft_queue_createt   hsa_queue_destroyt   hsa_queue_inactivatet!   hsa_queue_load_read_index_acquiret!   hsa_queue_load_read_index_relaxedt"   hsa_queue_load_write_index_acquiret"   hsa_queue_load_write_index_relaxedt#   hsa_queue_store_write_index_relaxedt#   hsa_queue_store_write_index_releaset!   hsa_queue_cas_write_index_acq_relt!   hsa_queue_cas_write_index_acquiret!   hsa_queue_cas_write_index_relaxedt!   hsa_queue_cas_write_index_releaset!   hsa_queue_add_write_index_acq_relt!   hsa_queue_add_write_index_acquiret!   hsa_queue_add_write_index_relaxedt!   hsa_queue_add_write_index_releaset"   hsa_queue_store_read_index_relaxedt"   hsa_queue_store_read_index_releaset   hsa_region_get_infot   hsa_agent_iterate_regionst   hsa_memory_allocatet   hsa_memory_freet   hsa_memory_copyt   hsa_memory_assign_agentt   hsa_memory_registert   hsa_memory_deregistert   hsa_isa_from_namet   hsa_isa_get_infot   hsa_isa_compatiblet   hsa_code_object_serializet   hsa_code_object_deserializet   hsa_code_object_destroyt   hsa_code_object_get_infot   hsa_code_object_get_symbolt   hsa_code_symbol_get_infot   hsa_code_object_iterate_symbolst   hsa_executable_createt   hsa_executable_destroyt   hsa_executable_load_code_objectt   hsa_executable_freezet   hsa_executable_get_infot%   hsa_executable_global_variable_definet+   hsa_executable_agent_global_variable_definet'   hsa_executable_readonly_variable_definet   hsa_executable_validatet   hsa_executable_get_symbolt   hsa_executable_symbol_get_infot   hsa_executable_iterate_symbolst   hsa_amd_coherency_get_typet&   hsa_amd_profiling_set_profiler_enabledt#   hsa_amd_profiling_get_dispatch_timet/   hsa_amd_profiling_convert_tick_to_system_domaint   hsa_amd_signal_async_handlert   hsa_amd_async_functiont   hsa_amd_signal_wait_anyt   hsa_amd_image_get_info_max_dimt   hsa_amd_queue_cu_set_maskt   hsa_amd_memory_pool_get_infot"   hsa_amd_agent_iterate_memory_poolst   hsa_amd_memory_pool_allocatet   hsa_amd_memory_pool_freet   hsa_amd_memory_async_copyt"   hsa_amd_agent_memory_pool_get_infot   hsa_amd_agents_allow_accesst   hsa_amd_memory_pool_can_migratet   hsa_amd_memory_migratet   hsa_amd_memory_lockt   hsa_amd_memory_unlockt   hsa_amd_interop_map_buffert   hsa_amd_image_create(   t
   __future__R    R   R   R   R   t    R   R   t   errorR   R   t   POINTERt   _PTRR-   t   handle_structt   c_intt   hsa_status_tt	   StructureR   t   hsa_access_permission_tt   hsa_endianness_tt   hsa_machine_model_tt   hsa_profile_tt   hsa_system_info_tt   hsa_extension_tt   hsa_agent_tt   hsa_agent_feature_tt   hsa_device_type_tt!   hsa_default_float_rounding_mode_tt   hsa_agent_info_tt   hsa_exception_policy_tR   t   HSA_LARGE_MODELR   t   hsa_signal_value_tt   hsa_signal_condition_tt   hsa_wait_state_tt   hsa_region_tR   t   hsa_queue_feature_tR   t   hsa_packet_type_tt   hsa_fence_scope_tt   hsa_packet_header_tt   hsa_packet_header_width_tt"   hsa_kernel_dispatch_packet_setup_tt(   hsa_kernel_dispatch_packet_setup_width_tR   R.   R1   t   hsa_barrier_or_packet_tt   hsa_region_segment_tt   hsa_region_global_flag_tt   hsa_region_info_tt   hsa_symbol_kind_tt   hsa_variable_allocation_tt   hsa_symbol_linkage_tt   hsa_variable_segment_tt	   hsa_isa_tt   hsa_isa_info_tt   hsa_code_object_tt   hsa_callback_data_tt   hsa_code_object_type_tt   hsa_code_object_info_tt   hsa_code_symbol_tt   hsa_code_symbol_info_tt   hsa_executable_tt   hsa_executable_state_tt   hsa_executable_info_tt   hsa_executable_symbol_tt   hsa_executable_symbol_info_tRB   RA   R7   t   BrigModule_tt   hsa_amd_agent_info_tt   hsa_amd_region_info_tt   hsa_amd_coherency_type_tRD   t	   CFUNCTYPEt   c_boolR   t   hsa_amd_signal_handlert   hsa_amd_segment_tt   hsa_amd_memory_pool_tt!   hsa_amd_memory_pool_global_flag_tt   hsa_amd_memory_pool_info_tt   hsa_amd_memory_pool_access_tt   hsa_amd_link_info_type_tt   hsa_amd_memory_pool_link_info_tt    hsa_amd_agent_memory_pool_info_tRG   t   hsa_ext_module_tt   hsa_ext_program_tt   hsa_ext_program_info_tt#   hsa_ext_finalizer_call_convention_tRK   t   c_char_pR\   R]   R^   t-   HSA_EXT_PROGRAM_ITERATE_MODULES_CALLBACK_FUNCR_   R`   t   c_int32Ra   RU   t   hsa_ext_image_tRn   Re   Rf   Rb   Rg   t   hsa_ext_image_capability_tRp   Rr   t   hsa_ext_sampler_tRz   Rx   Ry   Rt   t	   py_objectt   HSA_ITER_AGENT_CALLBACK_FUNCt   Nonet   HSA_QUEUE_CALLBACK_FUNCt'   HSA_AGENT_ITERATE_REGIONS_CALLBACK_FUNCt(   HSA_CODE_OBJECT_ITERATE_SYMBOLS_CALLBACKRo   t   HSA_ALLOC_CALLBACK_FUNCTIONt   void_fn_ptrt+   HSA_AMD_AGENT_ITERATE_MEMORY_POOLS_CALLBACKR   R   R   R   R,   t   API_PROTOTYPES(    (    (    s6   lib/python2.7/site-packages/numba/roc/hsadrv/drvapi.pyt   <module>   sΦ  																																																								
								
		




 
 
 
 



	


			

				
							