Commit Graph

3207 Commits

Author SHA1 Message Date
Alex Voicu 50265028fc Trailing whitespace is still not the final frontier. 2018-10-11 00:08:09 +01:00
Alex Voicu 3e4dbd32a1 Address Aaron's comments 2018-10-11 00:03:01 +01:00
Alex Voicu 069bbbd7ed Use HIP math functions, stop using hipLaunchParm. 2018-10-10 11:56:54 +01:00
Alex Voicu 4bc40551b5 Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_minimal_changes_for_hc_next 2018-10-10 11:44:09 +01:00
Alex Voicu ca375cb8c5 Re-sync with upstream. 2018-10-10 11:43:49 +01:00
Maneesh Gupta da64156fb2 Implementation for stream priority
- Requires ROCm 1.9.x or higher
- Requires HCC with PR#886 merged

Change-Id: Id7c95ea091ee610e80c9ad815f1cb989cba570ca
2018-10-05 16:27:46 +05:30
Aaron Enye Shi 0787f74ac2 Replace IRIF fences with atomic_work_item_fence 2018-10-04 21:47:28 +00:00
Jenkins 8f034cd0e2 Merge 'master' into 'amd-master'
Change-Id: I1884a7f1ee85ee14592fd6c2f28beb4872d0fd13
2018-10-04 04:09:36 -05:00
Maneesh Gupta 4ab45ef878 Merge pull request #697 from yxsamliu/dev-lib-path
Let hipcc add --hip-device-lib-path by default for hip-clang
2018-10-04 07:40:37 +05:30
Maneesh Gupta 651d08e750 Merge pull request #700 from ROCm-Developer-Tools/fix-long-long-decl
Fix hip_vector_types.h for long long vectors
2018-10-04 07:39:30 +05:30
Aaron Enye Shi 5dd35576f6 Fix hip_vector_types.h for long long vectors
There was a missing long in the declaration for [u]longlongN types.
2018-10-03 13:57:52 -04:00
Evgeny Mankov deafaa4417 Merge pull request #699 from emankov/master
[HIPIFY] CUDA 10.0 Driver API initial support
2018-10-03 20:33:37 +03:00
Evgeny Mankov e3d7cc2885 [HIPIFY] CUDA 10.0 Driver API initial support 2018-10-03 20:29:22 +03:00
Rahul Garg 5a3d89e99c Corrected the width calculation logic to accomodate multi channels 2018-10-03 12:07:38 +05:30
Yaxun Sam Liu 43402d5602 Let hipcc add --hip-device-lib-path by default for hip-clang
hip-clang by default assumes -fno-gpu-rdc, therefore requires
--hip-device-lib-path by default.
2018-10-01 15:14:54 -04:00
Yaxun Sam Liu dcc85be374 Add HIPCC_COMPILE_FLAGS_APPEND 2018-10-01 14:51:29 -04:00
Rahul Garg 0b8fc1d66a Fixed image width for linear resource type texture 2018-10-01 15:28:34 +05:30
Jenkins a39c70a2b2 Merge 'master' into 'amd-master'
Change-Id: I1cfb603a45cb6ffb834491ddd6f3ade667ab016c
2018-09-28 04:09:54 -05:00
Evgeny Mankov b4bef98707 Merge pull request #695 from emankov/master
[HIPIFY][cmake] CUDA 10.0 is not supported.
2018-09-27 19:08:58 +03:00
Evgeny Mankov d0c683fcde [HIPIFY][cmake] CUDA 10.0 is not supported. 2018-09-27 19:05:22 +03:00
Jenkins d0e0bebd46 Merge 'master' into 'amd-master'
Change-Id: Ieb0558a488ebf992a77c84ff4d81fba764a70401
2018-09-27 04:40:39 -05:00
Wen-Heng (Jack) Chung dd56942335 Keep the map which tracks GPU kernel symbols to grow monotonically 2018-09-26 19:49:02 +00:00
Wen-Heng (Jack) Chung 35c542b70f Improve performance of re-initialization logic
Keep track of shared libaries already discovered. Do not build HSA executables
for them.
2018-09-26 19:48:56 +00:00
Wen-Heng (Jack) Chung dab1a0f9db HIP program state re-initialization logic
This commit is to support kernels dynamically loaded thru means such as
dlopen() after HIP runtime initializes.
2018-09-26 19:48:47 +00:00
Evgeny Mankov 9ac5ac08fd Merge pull request #691 from emankov/docs
[HIPIFY][docs] Fix typos in Readme.md
2018-09-26 17:27:18 +03:00
Evgeny Mankov c943885a65 [HIPIFY][docs] Fix typos in Readme.md 2018-09-26 17:26:25 +03:00
Evgeny Mankov 23448bbf9b Merge pull request #690 from emankov/hipBLAS
[HIPIFY][doc] Update README.md due to new LLVM 7.0.0 and CUDA 10.0 re…
2018-09-26 17:05:47 +03:00
Evgeny Mankov 221ef1db1f [HIPIFY][doc] Update README.md due to new LLVM 7.0.0 and CUDA 10.0 releases. 2018-09-26 17:01:59 +03:00
Maneesh Gupta e7529f14b6 Merge pull request #689 from gargrahul/hipmemset_ret_success_sizezero
Return hipSuccess when sizeBytes=0 in hipMemset
2018-09-26 13:57:44 +05:30
Rahul Garg 90f57d452a Return hipSuccess when sizeBytes=0 in hipMemset 2018-09-26 12:47:36 +05:30
Maneesh Gupta 5c665acf74 Merge pull request #685 from ROCm-Developer-Tools/hip-trig-return
Improve hip_trig test case
2018-09-26 09:50:48 +05:30
Aaron Enye Shi 77c07d4118 Use sinf and cosf from ocml device libs
Using llvm_amdgcn builtin fails to produce accurate values, we should move to using the ocml device library versions.
2018-09-25 19:31:39 +00:00
Aaron Enye Shi 5179a72cda Use trig functions from ocml instead 2018-09-25 15:58:36 +00:00
Evgeny Mankov 3a1157653f Merge pull request #687 from emankov/hipBLAS
[HIPIFY][BLAS] Add support of hipblasGemmEx and corresponding types
2018-09-25 18:48:06 +03:00
Evgeny Mankov d279c7a1dd [HIPIFY][BLAS] Add support of hipblasGemmEx and corresponding types
TODO (hipBLAS/HIP): rename hipblasDatatype_t to hipDataType_t and move it from hipBLAS to HIP, as Data types are used not only in BLAS library.
2018-09-25 18:46:23 +03:00
Evgeny Mankov ea5eb8cd6a Merge pull request #686 from emankov/docs
[HIPIFY][docs] Update CUDNN_API_supported_by_HIP.md
2018-09-25 16:52:19 +03:00
Evgeny Mankov 4e06ab07e2 [HIPIFY][docs] Update CUDNN_API_supported_by_HIP.md 2018-09-25 16:50:40 +03:00
Jenkins eb1e00d503 Merge 'master' into 'amd-master'
Change-Id: Ida77d16d15313c8e52cdcb36b8e68e9d5c406256
2018-09-25 04:09:56 -05:00
Aaron Enye Shi 3d3820272a Fix missing HIP_ASSERT in hip_trig 2018-09-24 15:01:24 +00:00
Maneesh Gupta ca6b916d15 Merge pull request #683 from ROCm-Developer-Tools/hip-float-rounded
Disable non-default-rounded functions
2018-09-24 09:32:52 +05:30
Jenkins 91d77b2351 Merge 'master' into 'amd-master'
Change-Id: I3de7b9ac03c05e50e7fbdb855e120b2dff8d23b4
2018-09-23 20:41:55 -05:00
Aaron Enye Shi 357b6844fa Improve hip_trig test case
Hip_trig is failing but returning a passing value on HIP-Clang.  Also update with debug output and free arrays used.
2018-09-21 15:28:10 -04:00
Maneesh Gupta 0e3ba5a47d Merge pull request #684 from ROCm-Developer-Tools/mangupta-patch-2
[ci] Renable nvcc testing
2018-09-21 11:05:45 +05:30
Maneesh Gupta 255589ae15 Update hipTestFMA.cpp 2018-09-21 11:00:08 +05:30
Maneesh Gupta 6d794cd505 [ci] Renable nvcc testing
Change-Id: I7d720b41a3ddc99453fee8b9be30494bfec3a808
2018-09-21 10:11:31 +05:30
Aaron Enye Shi c11220f224 Disable non-default-rounded functions
Device library has removed the non-default-rounded functions, so hipFloatMath will fail to build. These include the removal of __ocml_sqrt_rte, __ocml_sqrt_rtn, __ocml_sqrt_rtp, and __ocml_sqrt_rtz. As seen here: https://github.com/RadeonOpenCompute/ROCm-Device-Libs/commit/2fc04e10e1354edee331ce700f98a60f8255effb . Disable these function tests for now, until they are re-enabled, or deleted completely.
2018-09-20 16:33:32 -04:00
Maneesh Gupta 3d67c9f952 Merge pull request #614 from ROCm-Developer-Tools/fma
Add overloading resolution functions for fma
2018-09-20 13:38:03 +05:30
Maneesh Gupta ecd6a212c7 Update hipTestFMA.cpp
Fix the test so that it works on nvcc path as well.
2018-09-20 11:23:51 +05:30
Maneesh Gupta 70b0b1d600 Merge pull request #682 from aaronenyeshi/hip-config-files
Create separate config files for hcc and clang
2018-09-20 11:21:31 +05:30
Maneesh Gupta 7f2be97667 Merge pull request #681 from yxsamliu/fix-warning-static
Silent warnings about duplicate static keyword
2018-09-20 07:59:10 +05:30