Граф коммитов

2913 Коммитов

Автор SHA1 Сообщение Дата
emankov 01a335b975 [HIPIFY] Add system includes for packaged hipify-clang to use it without the necessity of installing clang
Header files in those dirs are an integral part of clang, which includes wrapper headers for CUDA.
There is no need in checking those dirs.

[Reasons]
1. clang will not take into account empty or irrelevant include dirs;
2. Packages for different clang versions will have different header files in the above dirs.


[ROCm/hip commit: c519c89abf]
2018-12-29 21:53:18 +03:00
emankov 142d00b382 [HIPIFY] Get rid of setting '--cuda-gpu-arch='
[Reasons]
+ We don't compile kernel code at least for now as HIP kernel syntax is almost equal CUDA's;
+ clang always includes PTX in its binaries, so e.g. a binary compiled with --cuda-gpu-arch= would be forwards-compatible with e.g. sm_35 GPUs.


[ROCm/hip commit: dec459efca]
2018-12-29 19:48:28 +03:00
emankov 4e50eba101 [HIPIFY] Starts implicitly setting '-x cuda' by hipify-clang itself
+ No need in setting '-x cuda' for the user anymore;
+ Testing and Readme updated accordingly.


[ROCm/hip commit: 7ea586c323]
2018-12-29 17:04:59 +03:00
emankov d6593e4138 [HIPIFY][win] Set -std=c++14 if MSVC
+ Due to latest Windows SDK implementation based on c++14 features, '-std+c++14' is a must;
+ Doesn't affect older versions of MSVC 2017, 2015 (the latest supported is MSVC 2015);
+ On linux still '-std=c++11' is a must;
+ Exclude '-std=' from lit config.


[ROCm/hip commit: 2d3f62c3e1]
2018-12-29 15:51:06 +03:00
Evgeny Mankov fb905ba3cb Merge pull request #834 from emankov/master
[HIPIFY] LLVM compatibility

[ROCm/hip commit: 7cd4c4e9ac]
2018-12-28 15:13:36 +03:00
Maneesh Gupta 199a2c7189 [ci] Remove ROCm 1.9.x from test infrastructure
Change-Id: I58cce7c60f6def22f337bbe15fab2620419e202b


[ROCm/hip commit: d5d6541ad5]
2018-12-28 11:23:52 +05:30
emankov 279550644e [HIPIFY] LLVM compatibility
+ sys::fs::make_absolute fro LLVM < 5.0
+ sys::fs::real_path for LLVM >= 5.0


[ROCm/hip commit: 208d7cfaf1]
2018-12-28 01:34:35 +03:00
emankov eb90a74c3e [HIPIFY] Use sys::fs::createTemporaryFile without file creation
[Reasons]
+ File is opened further by clang
+ There is a regression with LLVM 5.x, when system error occurs: temporary file couldn't be renamed - permission denied.


[ROCm/hip commit: 912c4710ed]
2018-12-27 17:00:18 +03:00
Maneesh Gupta d109719178 Merge pull request #817 from aaronenyeshi/fix-rn-intrinsics
Add *_rn functions back into HIP intrinsics

[ROCm/hip commit: 8cbc3c49d2]
2018-12-27 16:07:27 +05:30
emankov 708367f299 [HIPIFY] Introduce option -o-dir
Option -o-dir for output directory:
  + if not specified source file(s) directory is used;
  + creates the directory if the directory doesn't exist (only one level in a tree);
  + if -o and -o-dir both are specified the hipified file is placed to "-o-dir" + "-o";
  + reports an error in case of a wrong directory specified, in case of necessity of creating a tree of subfolders, or in case of a filename specified.


[ROCm/hip commit: c8d720081f]
2018-12-26 16:30:41 +03:00
emankov f8f00472f8 [HIPIFY][#812] Finishing with temps
1. Option -temp-dir for temporary directory:
  + if not specified system temp is used;
  + creates the directory if the directory doesn't exist (only one level in a tree);
  + reports an error in case of a wrong directory specified, in case of necessity of creating a tree of subfolders, or in case of a filename specified.
2. Option -save-temps for preserving temporary files:
  + if specified temporary files are not being deleted from system temps and user temps as well.
3. Work with files in terms of calculated absolute paths by collapsing all '.' and '..' patterns, resolving symlinks and expanding '~' expression to the user's home directory:
  + to produce correct include paths;
  + to avoid possible errors on file routines.


[ROCm/hip commit: cc59af5dbd]
2018-12-22 00:47:19 +03:00
emankov 41901c007e [HIPIFY][fix][#824] Fix the bug with -inplace option
+ Do temp file copying instead of renaming
+ Replace all file routine functions with LLVM's
+ Do not output hipified file in case of errors


[ROCm/hip commit: 8bf3b42e7e]
2018-12-20 20:43:50 +03:00
emankov 13126143ed [HIPIFY] Add the legal right comment to all the sources
[ROCm/hip commit: fcaf954998]
2018-12-20 18:47:57 +03:00
Aaron Enye Shi 8e7b49d1cf Add *_rn functions back into HIP intrinsics
Add back the round-to-nearest-even intrinsics back to HIP math
intrinsics as it caused regression.


[ROCm/hip commit: 58dfeff27a]
2018-12-18 19:31:54 +00:00
Evgeny Mankov c0c5fbf0b7 [HIPIFY] Temporary files in system temps introducing
+ Files are not being placed near original source before hipification anymore, system tmp is used for them now.
+ Additional include (-I) to absolute original source dir is added
+ Partially implements #812
+ Tested on windows/linux, single/multiple inputs, with and without includes to user header files


[ROCm/hip commit: da6fdc0397]
2018-12-17 20:48:48 +03:00
Evgeny Mankov e29a80e5f2 [HIPIFY][fix] Fix for the rest of found bugs in Statistics
+ Signs of the converted file are extended
+ Total converted lines and total elapsed time are fixed
+ Zero rates are excluded from statistics


[ROCm/hip commit: bffacb6c72]
2018-12-13 18:35:45 +03:00
Evgeny Mankov 13faaec7b5 [HIPIFY][fix] Fixer for #801
[issue #801] Errors in hipification statistics


[ROCm/hip commit: 9d223f0f65]
2018-12-12 21:33:00 +03:00
Evgeny Mankov 2381e2a6ca Merge pull request #800 from emankov/master
[HIPIFY][tests][fix] Add correct CUDA version detection while testing

[ROCm/hip commit: 7741457dea]
2018-12-12 18:30:03 +03:00
Evgeny Mankov 237d9e2a37 [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


[ROCm/hip commit: 3d528cf491]
2018-12-12 17:05:01 +03:00
Maneesh Gupta 3cf96f31d0 Merge pull request #797 from gargrahul/fixhipPointerGetAttributes
Fixed hipPointerGetAttributes for hostmalloced ptr

[ROCm/hip commit: 56ce3e37d5]
2018-12-12 10:16:07 +05:30
Maneesh Gupta 07dcdff9e5 Merge pull request #608 from gargrahul/add_pinned_2d_sdma_copy
Added support for pinned 2D SDMA copy

[ROCm/hip commit: 0dd26b4f63]
2018-12-12 07:44:16 +05:30
Evgeny Mankov c91d1ef0db [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


[ROCm/hip commit: b955e317a7]
2018-12-11 22:03:11 +03:00
Rahul Garg b304ff5210 Fixed hipPointerGetAttributes for hostmalloced ptr
[ROCm/hip commit: 5f12067708]
2018-12-08 01:42:08 +05:30
Evgeny Mankov 3621afd4e6 [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


[ROCm/hip commit: c5ed25da22]
2018-12-06 21:52:54 +03:00
Evgeny Mankov 5cae606a0f [HIPIFY][tests] Reorganization
[ROCm/hip commit: 09612ac03f]
2018-12-04 20:47:34 +03:00
Evgeny Mankov fd03a77da0 [HIPIFY][SPARSE] Add 3 more CUDA 10.0 tests
+ lit update
+ fix typos


[ROCm/hip commit: 72d40db358]
2018-12-04 19:24:29 +03:00
Maneesh Gupta 98a6a29162 [ci] Add rocm-2.0.x to CI test infrastructure
Change-Id: I7fc0c40d1bf50a90ce3e210f2c8e83d1f4bf6d5c


[ROCm/hip commit: dc5b0a1fe0]
2018-12-03 08:54:13 +05:30
Evgeny Mankov 71005f60da [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


[ROCm/hip commit: 116b9191f7]
2018-11-30 15:33:57 +03:00
Siu Chi Chan bca8022aa0 Revert "Rely on code object metadat for kernarg arguments alignof and sizeof."
This reverts commit 6d64f5e112.


[ROCm/hip commit: 1fbf639962]
2018-11-29 11:38:37 -05:00
Siu Chi Chan a72a54996e Revert "Handle the very confusing dual encoding of the symbol name."
This reverts commit 2a69dd1fb6.


[ROCm/hip commit: 71189c10c1]
2018-11-29 11:38:36 -05:00
Siu Chi Chan 8bf51361e4 Revert "If we've already seen a __global__ function we do not need to re-parse"
This reverts commit d3beba42d3.


[ROCm/hip commit: 09f87e41d9]
2018-11-29 11:38:35 -05:00
Siu Chi Chan f04655ff6e Revert "Handle (odd) corner case of argumentless __global__ function."
This reverts commit 591d4d1b5f.


[ROCm/hip commit: aeca2c8cdc]
2018-11-29 11:38:34 -05:00
Siu Chi Chan a715dea79c Revert "Missing handling nullary __global__ functions for mixed arity cases."
This reverts commit 51c47fcc2e.


[ROCm/hip commit: 8eb9b38e76]
2018-11-29 11:38:31 -05:00
Siu Chi Chan 954535e0b5 Revert "Fix issue in kernarg metadata parsing due to early finalization"
This reverts commit 48c2d69d32.


[ROCm/hip commit: 909609773c]
2018-11-29 11:35:00 -05:00
Evgeny Mankov 2e10abdc53 [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


[ROCm/hip commit: 8a84c665e2]
2018-11-29 18:46:51 +03:00
Evgeny Mankov 9076aaed1f [HIPIFY][SPARSE] Preconditioners Reference: Incomplete LU Factorization: level 0
+ cuSPARSE_06 test
+ update CUSPARSE_API_supported_by_HIP.md


[ROCm/hip commit: 6c085c83a2]
2018-11-29 15:59:58 +03:00
Evgeny Mankov 27960048a3 [HIPIFY][SPARSE] Preconditioners Reference: Incomplete Cholesky Factorization: level 0
+ cuSPARSE_05 test
+ update CUSPARSE_API_supported_by_HIP.md


[ROCm/hip commit: b39bd8c9a9]
2018-11-28 20:10:30 +03:00
Maneesh Gupta 36d29ab65c Merge pull request #776 from yxsamliu/fix-vdi-path
Let hipcc handle HIP_VDI_HOME without x86_64

[ROCm/hip commit: 491caacff1]
2018-11-28 09:33:03 +05:30
Maneesh Gupta ba2d81a234 Merge pull request #761 from yxsamliu/genco
Let hip-clang support --genco

[ROCm/hip commit: 9f649333ab]
2018-11-28 09:32:56 +05:30
Yaxun Sam Liu 95802a836b Let hip-clang support --genco
[ROCm/hip commit: 450f093231]
2018-11-27 15:55:50 -05:00
Evgeny Mankov b2c7acb939 [HIPIFY][SPARSE] Extra functions
+ cuSPARSE_04 test
+ update CUSPARSE_API_supported_by_HIP.md


[ROCm/hip commit: 11fedfbff6]
2018-11-27 12:41:50 +03:00
Evgeny Mankov 1ceb4b3fb9 [HIPIFY][SPARSE] Level 3 functions
+ cuSPARSE_03 test
+ update CUSPARSE_API_supported_by_HIP.md


[ROCm/hip commit: 82bbaf0b70]
2018-11-27 11:57:25 +03:00
Yaxun Sam Liu f2c2af12b2 Let hipcc handle HIP_VDI_HOME without x86_64
[ROCm/hip commit: 9d46966a59]
2018-11-26 17:00:37 -05:00
Evgeny Mankov 171d7b4e45 [HIPIFY][SPARSE] Helper and Level 1,2 functions
+ 2 cuSPARSE tests
+ update CUSPARSE_API_supported_by_HIP.md


[ROCm/hip commit: c7f6266824]
2018-11-26 15:11:52 +03:00
Maneesh Gupta 28c52ae091 Merge pull request #772 from scchan/kernarg_metadata_early_finalize
Fix issue in kernarg metadata parsing due to early finalization

[ROCm/hip commit: 9a1d8137eb]
2018-11-26 08:55:19 +05:30
Maneesh Gupta e317a9a1fa Merge pull request #773 from fronteer/master
Support of printing process ID for HIP tracing 

[ROCm/hip commit: 7ce082415b]
2018-11-23 11:16:22 +05:30
Maneesh Gupta 05e09614be Merge pull request #760 from eshcherb/roctracer-hip-frontend-181113
Roctracer hip frontend 181113

[ROCm/hip commit: 160c509e23]
2018-11-23 11:08:25 +05:30
Evgeny 17ca5ddc41 FATAL_ERRROR if Profiling API header not found
[ROCm/hip commit: 8a4354bdc0]
2018-11-22 21:51:20 -06:00
Evgeny 367ac9788a fixing the adding of USE_PROF_API define only if the tracer header was found
[ROCm/hip commit: 3bcf2fcd18]
2018-11-22 21:12:08 -06:00
Qianfeng Zhang 724a1e6dc5 Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP
[ROCm/hip commit: 91e8ec9e4b]
2018-11-22 19:11:49 +08:00