AI/rocm-systems
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
3,138 Commits 3 Branches 0 Tags
8d28db9c8d07a9ef98d80cbb56ed30203fd17c10
Commit Graph

2897 Commits

Author SHA1 Message Date
Evgeny Mankov 8d28db9c8d [HIPIFY][fix] Fixer for #801 
[issue #801] Errors in hipification statistics
 2018-12-12 21:33:00 +03:00
Evgeny Mankov 80d5861d78 Merge pull request #800 from emankov/master 
[HIPIFY][tests][fix] Add correct CUDA version detection while testing
 2018-12-12 18:30:03 +03:00
Evgeny Mankov a5c66018b6 [HIPIFY][tests][fix] Add correct CUDA version detection while testing 
+ Just do load_config for lit.site.cfg earlier in lit.cfg to get initialized cuda_version
+ Remove lit.cfg.in for CMake variables substitution
+ Return back lit.cfg
+ Exclude CUDA 9.0 tests if CUDA < 9.0
+ Report CUDA version before running tests
 2018-12-12 17:05:01 +03:00
Maneesh Gupta a778f7cdf7 Merge pull request #797 from gargrahul/fixhipPointerGetAttributes 
Fixed hipPointerGetAttributes for hostmalloced ptr
 2018-12-12 10:16:07 +05:30
Maneesh Gupta 6ce99b066c Merge pull request #608 from gargrahul/add_pinned_2d_sdma_copy 
Added support for pinned 2D SDMA copy
 2018-12-12 07:44:16 +05:30
Evgeny Mankov 2b01f1eb6f [HIPIFY][tests][fix] Add correct CUDA version detection while testing 
+ Add lit.cfg.in for CMake variables substitution to now generated lit.cfg
+ Exclude lit.cfg
+ Exclude CUDA 9.0 tests if CUDA < 9.0
+ Report CUDA version before running tests
 2018-12-11 22:03:11 +03:00
Rahul Garg 77fd517e09 Fixed hipPointerGetAttributes for hostmalloced ptr 2018-12-08 01:42:08 +05:30
Evgeny Mankov 747eb2c11c [HIPIFY] Initial support of translation to ROCm 
+ Option '-roc' is added to translate to ROCm instead of HIP
+ Update hipification mechanism accordingly
+ Populate all translation maps with additional field for ROCm identifiers
+ There are 4 degrees of CUDA support now: full support, only by HIP, only by ROCm, unsupported
 2018-12-06 21:52:54 +03:00
Evgeny Mankov b76cf94562 [HIPIFY][tests] Reorganization 2018-12-04 20:47:34 +03:00
Evgeny Mankov a421aff96d [HIPIFY][SPARSE] Add 3 more CUDA 10.0 tests 
+ lit update
+ fix typos
 2018-12-04 19:24:29 +03:00
Maneesh Gupta 94292df570 [ci] Add rocm-2.0.x to CI test infrastructure 
Change-Id: I7fc0c40d1bf50a90ce3e210f2c8e83d1f4bf6d5c
 2018-12-03 08:54:13 +05:30
Evgeny Mankov 424e4c8229 [HIPIFY][SPARSE] Matrix Reorderings and Format Conversion Reference 
+ cuSPARSE is supported up to CUDA 10.0
+ cuSPARSE_08 test (CUDA 10.0)
+ update CUSPARSE_API_supported_by_HIP.md
+ lit: add a rule for CUDA 10.0 tests excluding
 2018-11-30 15:33:57 +03:00
Siu Chi Chan 4251a70bc0 Revert "Rely on code object metadat for kernarg arguments alignof and sizeof." 
This reverts commit 299b9d1382.
 2018-11-29 11:38:37 -05:00
Siu Chi Chan a41bce5163 Revert "Handle the very confusing dual encoding of the symbol name." 
This reverts commit 1fe33b4738.
 2018-11-29 11:38:36 -05:00
Siu Chi Chan dc36c49212 Revert "If we've already seen a __global__ function we do not need to re-parse" 
This reverts commit 1621deee71.
 2018-11-29 11:38:35 -05:00
Siu Chi Chan 30a9be5643 Revert "Handle (odd) corner case of argumentless __global__ function." 
This reverts commit 927b06f8d4.
 2018-11-29 11:38:34 -05:00
Siu Chi Chan c5df445d1f Revert "Missing handling nullary __global__ functions for mixed arity cases." 
This reverts commit 1e64813716.
 2018-11-29 11:38:31 -05:00
Siu Chi Chan adbf0c444b Revert "Fix issue in kernarg metadata parsing due to early finalization" 
This reverts commit ba2b5ff9da.
 2018-11-29 11:35:00 -05:00
Evgeny Mankov e8054fe485 [HIPIFY][SPARSE] Preconditioners Reference: Tridiagonal and Pentadiagonal solves 
+ Tridiagonal Solve, Batched Tridiagonal and Pentadiagonal Solve
+ cuSPARSE_07 test
+ update CUSPARSE_API_supported_by_HIP.md
 2018-11-29 18:46:51 +03:00
Evgeny Mankov ef99d6dee4 [HIPIFY][SPARSE] Preconditioners Reference: Incomplete LU Factorization: level 0 
+ cuSPARSE_06 test
+ update CUSPARSE_API_supported_by_HIP.md
 2018-11-29 15:59:58 +03:00
Evgeny Mankov e90373c927 [HIPIFY][SPARSE] Preconditioners Reference: Incomplete Cholesky Factorization: level 0 
+ cuSPARSE_05 test
+ update CUSPARSE_API_supported_by_HIP.md
 2018-11-28 20:10:30 +03:00
Maneesh Gupta a2de2a40d9 Merge pull request #776 from yxsamliu/fix-vdi-path 
Let hipcc handle HIP_VDI_HOME without x86_64
 2018-11-28 09:33:03 +05:30
Maneesh Gupta 3dcf68fe79 Merge pull request #761 from yxsamliu/genco 
Let hip-clang support --genco
 2018-11-28 09:32:56 +05:30
Yaxun Sam Liu 988dcd1e4a Let hip-clang support --genco 2018-11-27 15:55:50 -05:00
Evgeny Mankov c75b3c444b [HIPIFY][SPARSE] Extra functions 
+ cuSPARSE_04 test
+ update CUSPARSE_API_supported_by_HIP.md
 2018-11-27 12:41:50 +03:00
Evgeny Mankov a384efcecf [HIPIFY][SPARSE] Level 3 functions 
+ cuSPARSE_03 test
+ update CUSPARSE_API_supported_by_HIP.md
 2018-11-27 11:57:25 +03:00
Yaxun Sam Liu 0e8bc94a3f Let hipcc handle HIP_VDI_HOME without x86_64 2018-11-26 17:00:37 -05:00
Evgeny Mankov a04788ffa7 [HIPIFY][SPARSE] Helper and Level 1,2 functions 
+ 2 cuSPARSE tests
+ update CUSPARSE_API_supported_by_HIP.md
 2018-11-26 15:11:52 +03:00
Maneesh Gupta 3a41a8b1f1 Merge pull request #772 from scchan/kernarg_metadata_early_finalize 
Fix issue in kernarg metadata parsing due to early finalization
 2018-11-26 08:55:19 +05:30
Maneesh Gupta 5bfde06bcc Merge pull request #773 from fronteer/master 
Support of printing process ID for HIP tracing
 2018-11-23 11:16:22 +05:30
Maneesh Gupta 99bb89b756 Merge pull request #760 from eshcherb/roctracer-hip-frontend-181113 
Roctracer hip frontend 181113
 2018-11-23 11:08:25 +05:30
Evgeny c37c1288db FATAL_ERRROR if Profiling API header not found 2018-11-22 21:51:20 -06:00
Evgeny 37dcb91eef fixing the adding of USE_PROF_API define only if the tracer header was found 2018-11-22 21:12:08 -06:00
Qianfeng Zhang 4f85e98384 Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP 2018-11-22 19:11:49 +08:00
Qianfeng Zhang b88c8769ea Add support of printing process ID for HIP Tracing 2018-11-22 18:58:06 +08:00
Siu Chi Chan ba2b5ff9da Fix issue in kernarg metadata parsing due to early finalization 
The logic to parse the kernel metadata is unaware that enabling
of early finalization could result in multiple code blobs in a
single .kernel section.  This teaches the HIP runtime to handle
that.

Change-Id: I1581b42f0da8b30233d7898014f7468728c1d489
 2018-11-21 12:09:46 -05:00
Maneesh Gupta 40d3184dd1 Merge pull request #748 from mkuron/getsymboladdress 
Implement hipGetSymbolAddress and hipGetSymbolSize
 2018-11-21 10:32:01 +05:30
Maneesh Gupta 29083e2375 Merge pull request #763 from gargrahul/fix_hiphostregister 
Fix hipHostRegister
 2018-11-21 07:28:23 +05:30
emankov 732374233c [HIPIFY][SPARSE] Data types support 
+ Add all cuSPARSE types
+ Update CUSPARSE_API_supported_by_HIP.md
+ Update README.md
 2018-11-21 01:31:02 +03:00
emankov f66388bd05 [HIPIFY][SPARSE] Initial support 2018-11-20 17:58:05 +03:00
Michael Kuron e9b88711e2 Merge branch 'master' into getsymboladdress 2018-11-20 12:03:22 +01:00
Maneesh Gupta 7eaf20ed8c Merge pull request #765 from mangupta/jenkins-renable-alltests 
[ci] Renable excluded tests
 2018-11-20 11:56:50 +05:30
Evgeny Mankov d28c89830d [HIPIFY] Move Complex API types and functions to separate files 2018-11-19 21:04:47 +03:00
Evgeny Mankov 1472478194 [HIPIFY] CUDA Driver API functions total revise (up to CUDA 10.0) 
+ for all CUDA versions
+ add missing types
+ fix typos
+ sync with HIP
+ update CUDA_Driver_API_functions_supported_by_HIP.md
+ formatting, annotating
 2018-11-19 20:00:05 +03:00
Maneesh Gupta bb93474e05 [ci] Renable excluded tests 
Regressions caused by dependent components have been fixed or workaround
put in place.

Change-Id: I9ecaf0a4a645d9222f12d2c45291f2b23984b72b
 2018-11-19 14:31:48 +05:30
Rahul Garg aae87e21d2 Fix hipHostRegister 2018-11-17 05:38:35 +05:30
Evgeny Mankov b087a7f275 [HIPIFY][LLVMCompat] support of upcoming LLVM 8.0 
+ StringRef issue, which is finally moved to LLVM from Clang
+ Renamed getBeginLoc() and getEndLoc() resolution for Expr and TypeLoc classes
+ Support all the previous LLVM versions via LLVCompat
 2018-11-16 01:23:25 +03:00
Michael Kuron f71b8cbc7d Fix hipGetSymbolAddress/hipGetSymbolSize on nvcc 2018-11-15 09:48:00 +01:00
Maneesh Gupta 1685d3d0fd Merge pull request #758 from yxsamliu/fix-sample-module 
Fix sample bit_extract for hip-clang
 2018-11-14 13:22:45 +05:30
Maneesh Gupta 0c72d32b44 Merge pull request #756 from yxsamliu/fix-heap 
Define __hip_device_heap in header for hip-clang only
 2018-11-14 13:22:31 +05:30