U <c@sUddlZddlZddlZddlmZddgZgZeeed<ej dej dZ ej dej dZ ee e d d d Zed d dZdddZddZddZedkreZeedkrdnddS)N)List#check_code_for_cuda_kernel_launchescheck_cuda_kernel_launches exclude_filesz^.*<<<[^>]+>>>\s*\()flagsz/\s*;(?![^;}]*C10_CUDA_KERNEL_LAUNCH_CHECK\(\);))sstartposreturncCsdd}t||dD]B\}}|dkr.|d7}q|dkr|d8}|dkr||dSqtddS)zGiven a string "prefix (unknown number of characters) suffix" and the position of the first `(` returns the index of the character 1 past the `)`, accounting for paren nesting rN()zClosing parens not found!) enumerate IndexError)rrZopeningicrQ/tmp/pip-unpacked-wheel-gikjz4vx/torch/testing/_internal/check_kernel_launches.pyfind_matching_paren.s r)r cCstD]}||rdSqdS)NTF)rendswith)filenameZexclude_suffixrrrshould_exclude_file?s rcCs|dkr d}t|d}dd|D}d|}d}t|D]X}t||d}t||r@|d7}|| |d}t d|d |t j d q@|S) aEChecks code for CUDA kernel launches without cuda error checks. Args: filename - Filename of file containing the code. Used only for display purposes, so you can put anything here. code - The code to check Returns: The number of unsafe kernel launches in the code Nz##Python Function Call## cSsg|]\}}|d|qS)z: r).0linenoZlinecoderrr Wsz7check_code_for_cuda_kernel_launches..rr z)Missing C10_CUDA_KERNEL_LAUNCH_CHECK in 'z '. Context: file) r splitjoinkernel_launch_startfinditerrend has_checkmatchstartprintsysstderr)coderZnum_launches_without_checksmZ end_parencontextrrrrFs   c CsP|ds|dsdSt|r$dSt|d}|}t||}W5QRX|S)zChecks a file for CUDA kernel launches without cuda error checks Args: filename - File to check Returns: The number of unsafe kernel launches in the file z.cuz.cuhrr)rropenreadr)rfocontentsZ unsafeCountrrr check_filees  r0c Cs"tjtjt}tj|}tj|}d}g}t|D]v\}}}|tj|dksl|tj|dkrzg|dd<q>|D]4}tj||}t|}|dkr~||7}||q~q>|dkrd|dt |d} t | t j dt d t j d|D]}t d |t j dqt | t j d|S) zChecks all pytorch code for CUDA kernel launches without cuda error checks Returns: The number of unsafe kernel launches in the codebase rbuildz torch/includeNzFound z instances in z0 files where kernel launches didn't have checks.rzFiles without checks: ) ospathdirnamerealpath__file__walkrr0appendlenr%r&r') Z torch_dirZkernels_without_checksZfiles_without_checksrootdirnames filenamesxrZ file_resultZ count_strrrrrxs.  $  __main__r )N)r3rer&typingr__all__rstr__annotations__compile MULTILINErr"intrboolrrr0r__name__Zunsafe_launchesexitrrrrs0   )