Grafico dei commit

2924 Commit

Autore SHA1 Messaggio Data
emankov e8d2dab718 [HIPIFY][tests] Exclude CUDA 8.0 (9.0) tests if CUDA < 8.0 (9.0)
[ROCm/clr commit: 852bc8d545]
2019-01-03 18:06:49 +03:00
emankov 18ce5086c5 [HIPIFY][tests] Reduce cudaRegister.cu test
[ROCm/clr commit: 410f8f0b92]
2019-01-03 17:17:21 +03:00
Alex Voicu cfed8191f1 Hook into the creaky lazy-reinit machinery. Try to minimise race-risk.
[ROCm/clr commit: 3470692998]
2019-01-01 11:01:16 +05:30
Alex Voicu 6e61270569 More blobs, more problems.
[ROCm/clr commit: b2f76123b1]
2019-01-01 11:01:07 +05:30
Alex Voicu eebc544c62 Start re-working 731 for 2.0.
[ROCm/clr commit: 3e8f198b58]
2019-01-01 11:00:57 +05:30
Maneesh Gupta 5b8b5b842b Merge pull request #818 from yxsamliu/fix-hip-config
Add default arguments for hipConfigureCall

[ROCm/clr commit: aa932d542a]
2019-01-01 10:25:25 +05:30
Yaxun Sam Liu b2d9783c2f Use __dparm for default parameter
[ROCm/clr commit: 57d1f6e6cb]
2018-12-31 13:07:19 -05:00
Maneesh Gupta 389ef21eca Merge pull request #821 from gargrahul/remove_redundancy_memset3d_test
[dtest] Remove redundant arguments from hipMemset3D test

[ROCm/clr commit: 7647bdb664]
2018-12-31 15:32:19 +05:30
emankov a8a2395057 [HIPIFY][fix] Change system includes order
'include/cuda_wrappers' should go first.


[ROCm/clr commit: 158b358c5b]
2018-12-29 22:10:00 +03:00
emankov 4c5a332edc [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/clr commit: e9589e3330]
2018-12-29 21:53:18 +03:00
emankov 170add36d8 [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/clr commit: 6f6228cf36]
2018-12-29 19:48:28 +03:00
emankov 843f936503 [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/clr commit: cea1e5a1a6]
2018-12-29 17:04:59 +03:00
emankov 1e3c49e8f2 [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/clr commit: b24e89b40f]
2018-12-29 15:51:06 +03:00
Evgeny Mankov 35bc69677a Merge pull request #834 from emankov/master
[HIPIFY] LLVM compatibility

[ROCm/clr commit: 323e22e5fc]
2018-12-28 15:13:36 +03:00
Maneesh Gupta 78235295f6 [ci] Remove ROCm 1.9.x from test infrastructure
Change-Id: I58cce7c60f6def22f337bbe15fab2620419e202b


[ROCm/clr commit: 61e0546120]
2018-12-28 11:23:52 +05:30
emankov 725f821629 [HIPIFY] LLVM compatibility
+ sys::fs::make_absolute fro LLVM < 5.0
+ sys::fs::real_path for LLVM >= 5.0


[ROCm/clr commit: 723c58afa4]
2018-12-28 01:34:35 +03:00
emankov 1ff4bf47c6 [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/clr commit: 8f415def6f]
2018-12-27 17:00:18 +03:00
Maneesh Gupta 0a9a2d030b Merge pull request #817 from aaronenyeshi/fix-rn-intrinsics
Add *_rn functions back into HIP intrinsics

[ROCm/clr commit: 274db66ff2]
2018-12-27 16:07:27 +05:30
emankov c65d6a9e7a [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/clr commit: c65338fbf7]
2018-12-26 16:30:41 +03:00
emankov 0056b8ad20 [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/clr commit: 7cac7dbfea]
2018-12-22 00:47:19 +03:00
emankov 369ac7b6f5 [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/clr commit: cb598445f5]
2018-12-20 20:43:50 +03:00
emankov 7d9eaec992 [HIPIFY] Add the legal right comment to all the sources
[ROCm/clr commit: 340550cc56]
2018-12-20 18:47:57 +03:00
Rahul Garg 489f3ef7ba Remove redundant arguments from hipMemset3D test
[ROCm/clr commit: 10d2a9a269]
2018-12-20 06:51:22 +05:30
Yaxun Sam Liu 51702bed29 Add default arguments for hipConfigureCall
[ROCm/clr commit: 02deeadaa4]
2018-12-18 15:48:21 -05:00
Aaron Enye Shi 56262f0970 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/clr commit: 2d50392c17]
2018-12-18 19:31:54 +00:00
Evgeny Mankov 47d5d2cfd7 [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/clr commit: 1180928408]
2018-12-17 20:48:48 +03:00
Evgeny Mankov 882620028c [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/clr commit: 1e30cd3ea7]
2018-12-13 18:35:45 +03:00
Evgeny Mankov d2e478546b [HIPIFY][fix] Fixer for #801
[issue #801] Errors in hipification statistics


[ROCm/clr commit: 8d28db9c8d]
2018-12-12 21:33:00 +03:00
Evgeny Mankov a8980580c0 Merge pull request #800 from emankov/master
[HIPIFY][tests][fix] Add correct CUDA version detection while testing

[ROCm/clr commit: 80d5861d78]
2018-12-12 18:30:03 +03:00
Evgeny Mankov 0d92c82f79 [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/clr commit: a5c66018b6]
2018-12-12 17:05:01 +03:00
Maneesh Gupta f096437107 Merge pull request #797 from gargrahul/fixhipPointerGetAttributes
Fixed hipPointerGetAttributes for hostmalloced ptr

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

[ROCm/clr commit: 6ce99b066c]
2018-12-12 07:44:16 +05:30
Evgeny Mankov d38bbc99aa [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/clr commit: 2b01f1eb6f]
2018-12-11 22:03:11 +03:00
Rahul Garg 514e5a41e3 Fixed hipPointerGetAttributes for hostmalloced ptr
[ROCm/clr commit: 77fd517e09]
2018-12-08 01:42:08 +05:30
Evgeny Mankov ccad9cbd80 [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/clr commit: 747eb2c11c]
2018-12-06 21:52:54 +03:00
Evgeny Mankov 27496f1d0d [HIPIFY][tests] Reorganization
[ROCm/clr commit: b76cf94562]
2018-12-04 20:47:34 +03:00
Evgeny Mankov c6efca710f [HIPIFY][SPARSE] Add 3 more CUDA 10.0 tests
+ lit update
+ fix typos


[ROCm/clr commit: a421aff96d]
2018-12-04 19:24:29 +03:00
Maneesh Gupta feefdd498b [ci] Add rocm-2.0.x to CI test infrastructure
Change-Id: I7fc0c40d1bf50a90ce3e210f2c8e83d1f4bf6d5c


[ROCm/clr commit: 94292df570]
2018-12-03 08:54:13 +05:30
Evgeny Mankov d3ffb890c0 [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/clr commit: 424e4c8229]
2018-11-30 15:33:57 +03:00
Siu Chi Chan bda6edc929 Revert "Rely on code object metadat for kernarg arguments alignof and sizeof."
This reverts commit 1ec78f6d67.


[ROCm/clr commit: 4251a70bc0]
2018-11-29 11:38:37 -05:00
Siu Chi Chan b47617dd72 Revert "Handle the very confusing dual encoding of the symbol name."
This reverts commit 8599d053b4.


[ROCm/clr commit: a41bce5163]
2018-11-29 11:38:36 -05:00
Siu Chi Chan 9b6b628695 Revert "If we've already seen a __global__ function we do not need to re-parse"
This reverts commit 58c5dedc16.


[ROCm/clr commit: dc36c49212]
2018-11-29 11:38:35 -05:00
Siu Chi Chan 732088e131 Revert "Handle (odd) corner case of argumentless __global__ function."
This reverts commit f843c8dd48.


[ROCm/clr commit: 30a9be5643]
2018-11-29 11:38:34 -05:00
Siu Chi Chan 44ac74c9db Revert "Missing handling nullary __global__ functions for mixed arity cases."
This reverts commit 5647e0ae35.


[ROCm/clr commit: c5df445d1f]
2018-11-29 11:38:31 -05:00
Siu Chi Chan 61785e9d39 Revert "Fix issue in kernarg metadata parsing due to early finalization"
This reverts commit 0c610f5890.


[ROCm/clr commit: adbf0c444b]
2018-11-29 11:35:00 -05:00
Evgeny Mankov 1c4d1bf7a6 [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/clr commit: e8054fe485]
2018-11-29 18:46:51 +03:00
Evgeny Mankov 81004dc3ac [HIPIFY][SPARSE] Preconditioners Reference: Incomplete LU Factorization: level 0
+ cuSPARSE_06 test
+ update CUSPARSE_API_supported_by_HIP.md


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


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

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

[ROCm/clr commit: 3dcf68fe79]
2018-11-28 09:32:56 +05:30