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

2825 Commits

Author SHA1 Message Date
Alex Voicu 01ec23538e Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_get_alignment_and_size_from_metadata 2018-11-11 22:37:09 +00:00
Maneesh Gupta 826e0653bb Merge pull request #753 from yxsamliu/fatbin 
Add more checks for fatbin
 2018-11-09 06:26:43 +05:30
Yaxun Sam Liu 8fef5618ed Let hipcc handle clang-offload-bundler file in obj format for hip-clang 2018-11-08 16:50:34 -05:00
Yaxun Sam Liu 80b382a37a Add more checks for fatbin 2018-11-08 16:46:01 -05:00
Alex Voicu 392e2ba1ba Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_get_alignment_and_size_from_metadata 2018-11-08 06:53:06 -08:00
Maneesh Gupta e510be9395 Merge pull request #730 from yxsamliu/dbg-fatbin 
Add more checks and debug outputs for fat binary
 2018-11-08 11:44:27 +05:30
Maneesh Gupta 0bafc38135 Merge pull request #721 from fronteer/my-fix 
Make correct checking of the returned hipDeviceptr_t from read_global…
 2018-11-08 11:42:08 +05:30
Maneesh Gupta 8b1544c911 Merge pull request #742 from gargrahul/fix_module_global_tracking 
Fixes global symbols tracking in hip_module
 2018-11-08 11:41:35 +05:30
Aaron Enye Shi 7b3bbc85c5 Guard rcp rounded implementation as well 
Since rcp implementations of non-default rounded versions are not correct or supported in OCML, guard them using the same macro OCML_BASIC_ROUNDED_OPERATIONS. Also update the docs and tests.
 2018-11-06 19:53:28 +00:00
Aaron Enye Shi 9aa92238ab Guard the OCML rounded operations instead 
Instead of commenting all these functions out, guard the functions with a macro OCML_BASIC_ROUNDED_OPERATIONS.
 2018-11-06 16:32:14 +00:00
Aaron Enye Shi 789814ab30 Update hip-math-api doc to remove non-default-rounded 2018-11-05 22:54:55 +00:00
Aaron Enye Shi cef6e8ef1f Remove non-working non-default-rounded math apis 
In ROCm-Device-Libs, they have dropped the non-default-rounded versions of add, sub, mul, div, sqrt and fma. Therefore, ocml has removed the rte, rtp, rtn, and rtz counterparts. This will remove the same math APIs in HIP for _ru, _rd, _rn, and _rz.
 2018-11-05 22:34:16 +00:00
Alex Voicu 1c525d7222 Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_get_alignment_and_size_from_metadata 2018-11-01 23:17:27 +00:00
Siu Chi Chan cdd0109e70 Move the global arrays for hip malloc/free 
from a header into a source file such that
there's only an unique copy in an executable
and prevent wasting static memory on the host

Change-Id: Id5b62766f77809c8d7b47892cb7149c490dcbdb9
 2018-11-01 16:20:35 -04:00
Evgeny Mankov 83d1b50615 [HIPIFY][doc] Update README.md 
+ Split Linux and Windows sections
+ Rewrite Testing section
 2018-11-01 19:11:40 +03:00
Evgeny Mankov 48abb4a36b [HIPIFY][fix] Fix typo and functions' string arguments 
+ Fix typo with missing comma in counterNames array
+ Change std::string argument to const std::string& argument in all functions
 2018-11-01 16:57:57 +03:00
Jeff Daily 6eac038694 typedef struct hipFuncAttributes now C compatible. 
Fixes #591.
Fixes #694.
 2018-10-31 14:12:45 +05:30
Maneesh Gupta a75d4c0ecc Merge pull request #733 from ex-rzr/fix_array_alloc_size 
Fix allocation size of arrays with multiple and/or non-32-bit channels
 2018-10-31 14:08:58 +05:30
Maneesh Gupta c7f2198c6e Merge pull request #714 from aaronenyeshi/remove-static-hip-device 
Remove libhip_device.a static library
 2018-10-31 14:08:29 +05:30
Maneesh Gupta 8f667984af Merge pull request #713 from scchan/master-hcc_early_finalize_support 
Support more than one device code blobs in a single .kernel section
 2018-10-31 14:04:06 +05:30
Alex Voicu 000766850d Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_get_alignment_and_size_from_metadata 2018-10-30 23:34:46 +00:00
Alex Voicu 1621deee71 If we've already seen a __global__ function we do not need to re-parse 2018-10-30 23:34:27 +00:00
Rahul Garg 592efa017f Fixes global symbols tracking in hip_module 2018-10-31 03:22:38 +05:30
Evgeny Mankov ec68fda25a Merge pull request #741 from emankov/master 
[HIPIFY][fix][#739] Fix garbage after replacements
 2018-10-30 19:37:19 +03:00
Evgeny Mankov 2ab8e92195 [HIPIFY][fix][#739] Fix garbage after replacements 
[Issue] https://github.com/ROCm-Developer-Tools/HIP/issues/739
[Resolution] Always use an std::string not a clang::StringRef for replacement

P.S. Occurred only on Linux, on Windows works fine.
 2018-10-30 19:35:59 +03:00
Evgeny Mankov b2e6ce7be0 Merge pull request #740 from emankov/master 
[HIPIFY][fix] Return back cudaDeviceProp's struct field warpSize to hipWarpSize mapping
 2018-10-30 15:55:17 +03:00
Evgeny Mankov 3489fe9ca1 [HIPIFY][fix] Return back cudaDeviceProp's struct field warpSize to hipWarpSize mapping. 2018-10-30 15:53:00 +03:00
Maneesh Gupta a36889113c Merge pull request #726 from ROCm-Developer-Tools/feature_minimal_changes_for_hc_next 
hipLaunchKernel, hipLaunchParm are deprecated, and shall be removed.
 2018-10-30 09:20:39 +05:30
Alex Voicu 1fe33b4738 Handle the very confusing dual encoding of the symbol name. 2018-10-30 01:55:09 +00:00
Evgeny Mankov 2af2827a05 [HIPIFY] Modify HIP types to conform to CUDA's ones 2018-10-29 20:51:25 +03:00
Alex Voicu 0f911d7727 Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_get_alignment_and_size_from_metadata 2018-10-29 15:41:44 +00:00
Evgeny Mankov 41bc184e90 [HIPIFY] CUDA Runtime API data types total revise 
+ for all CUDA versions up to 10.0
+ add missing types
+ fix typos
+ sync with HIP
+ sync with CUDA Driver API
+ update CUDA_Runtime_API_functions_supported_by_HIP.md
+ update CUDA Driver API map accordingly
+ update CUDA_Driver_API_functions_supported_by_HIP.md
+ formatting, annotating
 2018-10-29 17:13:00 +03:00
Anton Gorenko 6e6297f3cd Fix allocation size of arrays with multiple and/or non-32-bit channels 
hipMallocArray and hipMalloc3DArray must use sum of bits
of all components.
 2018-10-29 18:12:00 +06:00
Alex Voicu b68caf7653 Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_get_alignment_and_size_from_metadata 2018-10-28 17:02:10 +00:00
Alex Voicu 299b9d1382 Rely on code object metadat for kernarg arguments alignof and sizeof. 2018-10-28 17:01:00 +00:00
Yaxun Sam Liu 0027a54d8b Add HIP_DUMP_CODE_OBJECT 2018-10-26 14:14:00 -04:00
Yaxun Sam Liu da6c5c152e Adding checks and debug output for fat binary for hip-clang 2018-10-26 14:13:12 -04:00
Evgeny Mankov 5ab9c4bbca [HIPIFY][doc] Readme update 
Clang 7.0.0 release has a known bug https://bugs.llvm.org/show_bug.cgi?id=36384, thus 7.0.0 is unstable release for Linux and Windows.
Last stable and tested LLVM+Clang release is 6.0.1.
 2018-10-26 15:01:58 +03:00
Aaron Enye Shi ba43d1ce1b Remove libhip_device.a static library 
Move remaining function definitions from device_util.cpp to hip_runtime.h header. We can now remove the static library completely as device_util.cpp was the last file part of target hip::hip_device .
 2018-10-25 19:52:35 +00:00
Evgeny Mankov b244d1fc99 [HIPIFY][cmake][fix] Mark all target_link_libraries with PRIVATE keyword 
[Reason]
Avoid cmake error occurred when mixing signatures with AddLLVM.cmake

[Error]
CMake Error at CMakeLists.txt:26 (target_link_libraries): The keyword signature for target_link_libraries has already been used with the target "hipify-clang".
All uses of target_link_libraries with a target must be either all-keyword or all-plain.

Error occurred only on Linux and LLVM 7.0.0
 2018-10-25 17:09:18 +03:00
Alex Voicu a743939900 hipLaunchKernel, hipLaunchParm are deprecated, and shall be removed. 2018-10-25 13:32:17 +01:00
Maneesh Gupta 05beeec84d Merge pull request #723 from mangupta/fix_double_shfl 
Fix logic for double variants of __shfl*
 2018-10-25 06:01:38 +05:30
Maneesh Gupta cd53504215 Merge pull request #720 from mangupta/make_rocm19_usable_again 
Make HIP functional again with HCC from ROCm 1.9.x
 2018-10-25 06:01:27 +05:30
Maneesh Gupta df02a8ef5f Merge pull request #716 from yxsamliu/gfx906 
Let hipcc handle gfx906 for hip-clang
 2018-10-25 06:01:16 +05:30
Maneesh Gupta 7b6d232672 Fix logic for double variants of __shfl* 
Change-Id: I604f00b54cf4bd9c5f26ca6fa680fca5e9629417
 2018-10-24 12:39:09 +05:30
Maneesh Gupta b01ac26948 Make HIP functional again with HCC from ROCm 1.9.x 
Change-Id: I214acdfd0b79dcf783993e44fe31baee64fd4dc3
 2018-10-24 10:41:56 +05:30
Qianfeng Zhang 443698ce00 Make correct checking of the returned hipDeviceptr_t from read_global_description() 2018-10-23 21:13:11 +08:00
Evgeny Mankov 75972cb51d [HIPIFY] Split CUDA2HIP map into a number of maps based on API type 
[Reasons]
+ Simplify the support
+ Optimize compilation and code generation time

[Additionally]
+ Update minimum required version of cmake
+ Fix MSVC compile options force update
 2018-10-23 00:00:10 +03:00
Yaxun Sam Liu 1f7b924e2e Let hipcc handle gfx906 for hip-clang 2018-10-21 10:04:30 -04:00
Maneesh Gupta 407e092a13 Merge pull request #705 from ROCm-Developer-Tools/feature_minimal_changes_for_hc_next 
Feature minimal changes for hc next
 2018-10-19 06:58:31 +05:30