Evgeny Mankov
506f2f4043
[HIPIFY] CUDA Driver API functions total revise (up to CUDA 10.0)
...
+ for all CUDA versions
+ add missing types
+ fix typos
+ sync with HIP
+ update CUDA_Driver_API_functions_supported_by_HIP.md
+ formatting, annotating
[ROCm/clr commit: 1472478194 ]
2018-11-19 20:00:05 +03:00
Evgeny Mankov
f94d93e5ed
Merge pull request #762 from emankov/master
...
[HIPIFY][LLVMCompat] Support of upcoming LLVM 8.0
[ROCm/clr commit: 8b0a55144f ]
2018-11-16 14:53:30 +03:00
Evgeny Mankov
1b6421eff6
[HIPIFY][LLVMCompat] support of upcoming LLVM 8.0
...
+ StringRef issue, which is finally moved to LLVM from Clang
+ Renamed getBeginLoc() and getEndLoc() resolution for Expr and TypeLoc classes
+ Support all the previous LLVM versions via LLVCompat
[ROCm/clr commit: b087a7f275 ]
2018-11-16 01:23:25 +03:00
Maneesh Gupta
119a8fba1a
Merge pull request #758 from yxsamliu/fix-sample-module
...
Fix sample bit_extract for hip-clang
[ROCm/clr commit: 1685d3d0fd ]
2018-11-14 13:22:45 +05:30
Maneesh Gupta
9b07e74cd3
Merge pull request #756 from yxsamliu/fix-heap
...
Define __hip_device_heap in header for hip-clang only
[ROCm/clr commit: 0c72d32b44 ]
2018-11-14 13:22:31 +05:30
Maneesh Gupta
21cbe24800
Merge pull request #755 from gargrahul/fix_memcpy_symb_nonzerodev
...
Fixed hipMemcpyToSymbol doesn't work on GPU other than device 0
[ROCm/clr commit: f769320b5c ]
2018-11-14 13:22:22 +05:30
Maneesh Gupta
2754a6c78b
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.
[ROCm/clr commit: c8e6e6e92d ]
2018-11-14 13:22:13 +05:30
Rahul Garg
ea9ea82fe1
Fixed symbol tracking device index
...
[ROCm/clr commit: 70bb04cc61 ]
2018-11-13 07:01:17 +05:30
Yaxun Sam Liu
e85fa43e53
Fix sample bit_extract for hip-clang
...
[ROCm/clr commit: de907674d6 ]
2018-11-12 16:50:47 -05:00
Yaxun Sam Liu
857cfa32c7
Define __hip_device_heap in header for hip-clang only
...
[ROCm/clr commit: c44f2795d5 ]
2018-11-12 16:39:41 -05:00
Rahul Garg
696a6df141
Fixed hipMemcpyToSymbol doesn't work on GPU other than device 0 SWDEV-166881
...
[ROCm/clr commit: ac32566d9b ]
2018-11-13 00:49:20 +05:30
Alex Voicu
5647e0ae35
Missing handling nullary __global__ functions for mixed arity cases.
...
[ROCm/clr commit: 1e64813716 ]
2018-11-12 01:51:59 +00:00
Alex Voicu
f843c8dd48
Handle (odd) corner case of argumentless __global__ function.
...
[ROCm/clr commit: 927b06f8d4 ]
2018-11-12 00:32:35 +00:00
Alex Voicu
0178ad536a
Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_get_alignment_and_size_from_metadata
...
[ROCm/clr commit: 01ec23538e ]
2018-11-11 22:37:09 +00:00
Maneesh Gupta
553721ef07
Merge pull request #753 from yxsamliu/fatbin
...
Add more checks for fatbin
[ROCm/clr commit: 826e0653bb ]
2018-11-09 06:26:43 +05:30
Maneesh Gupta
3d7d3f3f20
Merge pull request #752 from yxsamliu/fix-bundle
...
Let hipcc handle clang-offload-bundler file in obj format for hip-clang
[ROCm/clr commit: 02a0df641f ]
2018-11-09 06:26:32 +05:30
Yaxun Sam Liu
858b71b7bd
Let hipcc handle clang-offload-bundler file in obj format for hip-clang
...
[ROCm/clr commit: 8fef5618ed ]
2018-11-08 16:50:34 -05:00
Yaxun Sam Liu
5d54fe864f
Add more checks for fatbin
...
[ROCm/clr commit: 80b382a37a ]
2018-11-08 16:46:01 -05:00
Alex Voicu
c4acf6e8cc
Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_get_alignment_and_size_from_metadata
...
[ROCm/clr commit: 392e2ba1ba ]
2018-11-08 06:53:06 -08:00
Maneesh Gupta
a3758b506d
Merge pull request #730 from yxsamliu/dbg-fatbin
...
Add more checks and debug outputs for fat binary
[ROCm/clr commit: e510be9395 ]
2018-11-08 11:44:27 +05:30
Maneesh Gupta
387e6de9e6
Merge pull request #721 from fronteer/my-fix
...
Make correct checking of the returned hipDeviceptr_t from read_global…
[ROCm/clr commit: 0bafc38135 ]
2018-11-08 11:42:08 +05:30
Maneesh Gupta
46bf341c12
Merge pull request #742 from gargrahul/fix_module_global_tracking
...
Fixes global symbols tracking in hip_module
[ROCm/clr commit: 8b1544c911 ]
2018-11-08 11:41:35 +05:30
Maneesh Gupta
b8968b3f02
Merge pull request #750 from aaronenyeshi/remove-non-default-rounded-math
...
Remove non-default-rounded math apis
[ROCm/clr commit: 4ccea03e15 ]
2018-11-08 11:40:03 +05:30
Aaron Enye Shi
890beb81d6
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.
[ROCm/clr commit: 7b3bbc85c5 ]
2018-11-06 19:53:28 +00:00
Aaron Enye Shi
4480bb6d06
Guard the OCML rounded operations instead
...
Instead of commenting all these functions out, guard the functions with a macro OCML_BASIC_ROUNDED_OPERATIONS.
[ROCm/clr commit: 9aa92238ab ]
2018-11-06 16:32:14 +00:00
Aaron Enye Shi
4587e32e46
Update hip-math-api doc to remove non-default-rounded
...
[ROCm/clr commit: 789814ab30 ]
2018-11-05 22:54:55 +00:00
Aaron Enye Shi
5c1dc7a071
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.
[ROCm/clr commit: cef6e8ef1f ]
2018-11-05 22:34:16 +00:00
Maneesh Gupta
d3af333417
Merge pull request #747 from scchan/fix_hip_malloc_global_arrays
...
Move the global arrays for hip malloc/free
[ROCm/clr commit: 52b9a62e21 ]
2018-11-02 11:32:11 +05:30
Alex Voicu
e3c9869fbe
Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_get_alignment_and_size_from_metadata
...
[ROCm/clr commit: 1c525d7222 ]
2018-11-01 23:17:27 +00:00
Siu Chi Chan
e26a728173
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
[ROCm/clr commit: cdd0109e70 ]
2018-11-01 16:20:35 -04:00
Evgeny Mankov
f659cb5855
Merge pull request #746 from emankov/master
...
[HIPIFY][doc] Update README.md
[ROCm/clr commit: 9fe55a3d0d ]
2018-11-01 19:13:22 +03:00
Evgeny Mankov
77835ded3f
[HIPIFY][doc] Update README.md
...
+ Split Linux and Windows sections
+ Rewrite Testing section
[ROCm/clr commit: 83d1b50615 ]
2018-11-01 19:11:40 +03:00
Evgeny Mankov
221367ef4a
Merge pull request #745 from emankov/master
...
[HIPIFY][fix] Fix typo and functions' string arguments
[ROCm/clr commit: 27bb4808d9 ]
2018-11-01 17:03:01 +03:00
Evgeny Mankov
7b244965b6
[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
[ROCm/clr commit: 48abb4a36b ]
2018-11-01 16:57:57 +03:00
Maneesh Gupta
084830799b
Merge pull request #744 from mangupta/hipfuncattrib
...
typedef struct hipFuncAttributes now C compatible.
[ROCm/clr commit: 9fdc1cb875 ]
2018-10-31 16:25:25 +05:30
Jeff Daily
34c5d69f7c
typedef struct hipFuncAttributes now C compatible.
...
Fixes #591 .
Fixes #694 .
[ROCm/clr commit: 6eac038694 ]
2018-10-31 14:12:45 +05:30
Maneesh Gupta
7052a66935
Merge pull request #733 from ex-rzr/fix_array_alloc_size
...
Fix allocation size of arrays with multiple and/or non-32-bit channels
[ROCm/clr commit: a75d4c0ecc ]
2018-10-31 14:08:58 +05:30
Maneesh Gupta
130edf2c43
Merge pull request #714 from aaronenyeshi/remove-static-hip-device
...
Remove libhip_device.a static library
[ROCm/clr commit: c7f2198c6e ]
2018-10-31 14:08:29 +05:30
Maneesh Gupta
58aec2b859
Merge pull request #713 from scchan/master-hcc_early_finalize_support
...
Support more than one device code blobs in a single .kernel section
[ROCm/clr commit: 8f667984af ]
2018-10-31 14:04:06 +05:30
Alex Voicu
1c6b92bbfb
Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_get_alignment_and_size_from_metadata
...
[ROCm/clr commit: 000766850d ]
2018-10-30 23:34:46 +00:00
Alex Voicu
58c5dedc16
If we've already seen a __global__ function we do not need to re-parse
...
[ROCm/clr commit: 1621deee71 ]
2018-10-30 23:34:27 +00:00
Rahul Garg
8856b89b21
Fixes global symbols tracking in hip_module
...
[ROCm/clr commit: 592efa017f ]
2018-10-31 03:22:38 +05:30
Evgeny Mankov
5150bb398e
Merge pull request #741 from emankov/master
...
[HIPIFY][fix][#739 ] Fix garbage after replacements
[ROCm/clr commit: ec68fda25a ]
2018-10-30 19:37:19 +03:00
Evgeny Mankov
24bd6d2925
[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.
[ROCm/clr commit: 2ab8e92195 ]
2018-10-30 19:35:59 +03:00
Evgeny Mankov
c5db5e4c4a
Merge pull request #740 from emankov/master
...
[HIPIFY][fix] Return back cudaDeviceProp's struct field warpSize to hipWarpSize mapping
[ROCm/clr commit: b2e6ce7be0 ]
2018-10-30 15:55:17 +03:00
Evgeny Mankov
4ae4f1073f
[HIPIFY][fix] Return back cudaDeviceProp's struct field warpSize to hipWarpSize mapping.
...
[ROCm/clr commit: 3489fe9ca1 ]
2018-10-30 15:53:00 +03:00
Maneesh Gupta
73c69744d4
Merge pull request #726 from ROCm-Developer-Tools/feature_minimal_changes_for_hc_next
...
hipLaunchKernel, hipLaunchParm are deprecated, and shall be removed.
[ROCm/clr commit: a36889113c ]
2018-10-30 09:20:39 +05:30
Alex Voicu
8599d053b4
Handle the very confusing dual encoding of the symbol name.
...
[ROCm/clr commit: 1fe33b4738 ]
2018-10-30 01:55:09 +00:00
Evgeny Mankov
ab5f0e7c8f
Merge pull request #736 from emankov/master
...
[HIPIFY] Modify HIP types to conform to CUDA's ones
[ROCm/clr commit: 93d12de69e ]
2018-10-29 20:57:22 +03:00
Evgeny Mankov
8c98204b9c
[HIPIFY] Modify HIP types to conform to CUDA's ones
...
[ROCm/clr commit: 2af2827a05 ]
2018-10-29 20:51:25 +03:00