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

3058 Commits

This Branch
This Branch
All Branches
Author SHA1 Message Date
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
Maneesh Gupta f769320b5c Merge pull request #755 from gargrahul/fix_memcpy_symb_nonzerodev 
Fixed hipMemcpyToSymbol doesn't work on GPU other than device 0
 2018-11-14 13:22:22 +05:30
Maneesh Gupta c8e6e6e92d Merge pull request #731 from ROCm-Developer-Tools/feature_get_alignment_and_size_from_metadata 
Rely on code object metadata for kernarg arguments alignof and sizeof.
 2018-11-14 13:22:13 +05:30
Rahul Garg 70bb04cc61 Fixed symbol tracking device index 2018-11-13 07:01:17 +05:30
Yaxun Sam Liu de907674d6 Fix sample bit_extract for hip-clang 2018-11-12 16:50:47 -05:00
Yaxun Sam Liu c44f2795d5 Define __hip_device_heap in header for hip-clang only 2018-11-12 16:39:41 -05:00
Rahul Garg ac32566d9b Fixed hipMemcpyToSymbol doesn't work on GPU other than device 0 SWDEV-166881 2018-11-13 00:49:20 +05:30
Alex Voicu 1e64813716 Missing handling nullary __global__ functions for mixed arity cases. 2018-11-12 01:51:59 +00:00
Alex Voicu 927b06f8d4 Handle (odd) corner case of argumentless __global__ function. 2018-11-12 00:32:35 +00:00
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
Maneesh Gupta 02a0df641f Merge pull request #752 from yxsamliu/fix-bundle 
Let hipcc handle clang-offload-bundler file in obj format for hip-clang
 2018-11-09 06:26:32 +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
Maneesh Gupta 4ccea03e15 Merge pull request #750 from aaronenyeshi/remove-non-default-rounded-math 
Remove non-default-rounded math apis
 2018-11-08 11:40:03 +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
Maneesh Gupta 52b9a62e21 Merge pull request #747 from scchan/fix_hip_malloc_global_arrays 
Move the global arrays for hip malloc/free
 2018-11-02 11:32:11 +05:30
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 9fe55a3d0d Merge pull request #746 from emankov/master 
[HIPIFY][doc] Update README.md
 2018-11-01 19:13:22 +03: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 27bb4808d9 Merge pull request #745 from emankov/master 
[HIPIFY][fix] Fix typo and functions' string arguments
 2018-11-01 17:03:01 +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
Maneesh Gupta 9fdc1cb875 Merge pull request #744 from mangupta/hipfuncattrib 
typedef struct hipFuncAttributes now C compatible.
 2018-10-31 16:25:25 +05:30
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 93d12de69e Merge pull request #736 from emankov/master 
[HIPIFY] Modify HIP types to conform to CUDA's ones
 2018-10-29 20:57:22 +03: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 ce5269025c Merge pull request #734 from emankov/master 
[HIPIFY] CUDA Runtime API data types total revise
 2018-10-29 17:16:07 +03: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