Commit graph

3064 Commits

Autor SHA1 Nachricht Datum
Evgeny Mankov 5cbf1fcf58 Merge pull request #767 from emankov/master
[HIPIFY] Move Complex API types and functions to separate files

[ROCm/hip commit: 8f197f9072]
2018-11-19 21:07:03 +03:00
Evgeny Mankov 223ab79e90 [HIPIFY] Move Complex API types and functions to separate files
[ROCm/hip commit: 8aefe12b8e]
2018-11-19 21:04:47 +03:00
Evgeny Mankov a36bb84a81 Merge pull request #766 from emankov/master
[HIPIFY] CUDA Driver API functions total revise (up to CUDA 10.0)

[ROCm/hip commit: 99e3f376ee]
2018-11-19 20:02:20 +03:00
Evgeny Mankov b55426217c [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/hip commit: cfabad4354]
2018-11-19 20:00:05 +03:00
Evgeny Mankov 532737d329 Merge pull request #762 from emankov/master
[HIPIFY][LLVMCompat] Support of upcoming LLVM 8.0

[ROCm/hip commit: 32767e92bc]
2018-11-16 14:53:30 +03:00
Evgeny Mankov 517ba1c4c1 [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/hip commit: aad5858cb1]
2018-11-16 01:23:25 +03:00
Maneesh Gupta ee6e3d56c4 Merge pull request #758 from yxsamliu/fix-sample-module
Fix sample bit_extract for hip-clang

[ROCm/hip commit: 3a55519d6e]
2018-11-14 13:22:45 +05:30
Maneesh Gupta bc85e694c5 Merge pull request #756 from yxsamliu/fix-heap
Define __hip_device_heap in header for hip-clang only

[ROCm/hip commit: 0770c2b8da]
2018-11-14 13:22:31 +05:30
Maneesh Gupta 700a8183f8 Merge pull request #755 from gargrahul/fix_memcpy_symb_nonzerodev
Fixed hipMemcpyToSymbol doesn't work on GPU other than device 0

[ROCm/hip commit: b4e4aafc16]
2018-11-14 13:22:22 +05:30
Maneesh Gupta 6c0e4d191a 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/hip commit: 23f3e5d7d9]
2018-11-14 13:22:13 +05:30
Rahul Garg 30c4fd3875 Fixed symbol tracking device index
[ROCm/hip commit: 6b3cbc65ad]
2018-11-13 07:01:17 +05:30
Yaxun Sam Liu 69080f3cb4 Fix sample bit_extract for hip-clang
[ROCm/hip commit: bc40ddabe0]
2018-11-12 16:50:47 -05:00
Yaxun Sam Liu a30829a7bf Define __hip_device_heap in header for hip-clang only
[ROCm/hip commit: 17ac81b69e]
2018-11-12 16:39:41 -05:00
Rahul Garg ecea878072 Fixed hipMemcpyToSymbol doesn't work on GPU other than device 0 SWDEV-166881
[ROCm/hip commit: 11e7ab8879]
2018-11-13 00:49:20 +05:30
Alex Voicu 51c47fcc2e Missing handling nullary __global__ functions for mixed arity cases.
[ROCm/hip commit: 4ebc229b9a]
2018-11-12 01:51:59 +00:00
Alex Voicu 591d4d1b5f Handle (odd) corner case of argumentless __global__ function.
[ROCm/hip commit: c0bd1a5af8]
2018-11-12 00:32:35 +00:00
Alex Voicu 9698438260 Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_get_alignment_and_size_from_metadata
[ROCm/hip commit: eddb783e9b]
2018-11-11 22:37:09 +00:00
Maneesh Gupta c7e403e4d4 Merge pull request #753 from yxsamliu/fatbin
Add more checks for fatbin

[ROCm/hip commit: de54e92da2]
2018-11-09 06:26:43 +05:30
Maneesh Gupta 87c920b6be Merge pull request #752 from yxsamliu/fix-bundle
Let hipcc handle clang-offload-bundler file in obj format for hip-clang

[ROCm/hip commit: 5da6e46c68]
2018-11-09 06:26:32 +05:30
Yaxun Sam Liu a7f7a01513 Let hipcc handle clang-offload-bundler file in obj format for hip-clang
[ROCm/hip commit: 3d51a1fb01]
2018-11-08 16:50:34 -05:00
Yaxun Sam Liu aaf12143ae Add more checks for fatbin
[ROCm/hip commit: a31b6b78d5]
2018-11-08 16:46:01 -05:00
Alex Voicu 9e2269c8db Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_get_alignment_and_size_from_metadata
[ROCm/hip commit: aa6815cdc8]
2018-11-08 06:53:06 -08:00
Maneesh Gupta 774be2f94f Merge pull request #730 from yxsamliu/dbg-fatbin
Add more checks and debug outputs for fat binary

[ROCm/hip commit: 0a1584b075]
2018-11-08 11:44:27 +05:30
Maneesh Gupta e599773b9a Merge pull request #721 from fronteer/my-fix
Make correct checking of the returned hipDeviceptr_t from read_global…

[ROCm/hip commit: e672dc8a55]
2018-11-08 11:42:08 +05:30
Maneesh Gupta 79861d3eeb Merge pull request #742 from gargrahul/fix_module_global_tracking
Fixes global symbols tracking in hip_module

[ROCm/hip commit: 8d8d12f65d]
2018-11-08 11:41:35 +05:30
Maneesh Gupta bd46fd037d Merge pull request #750 from aaronenyeshi/remove-non-default-rounded-math
Remove non-default-rounded math apis

[ROCm/hip commit: 4862dcaf87]
2018-11-08 11:40:03 +05:30
Aaron Enye Shi 8bf2429663 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/hip commit: 0cfaa52d15]
2018-11-06 19:53:28 +00:00
Aaron Enye Shi eb4053e3fe Guard the OCML rounded operations instead
Instead of commenting all these functions out, guard the functions with a macro OCML_BASIC_ROUNDED_OPERATIONS.


[ROCm/hip commit: e59c33250a]
2018-11-06 16:32:14 +00:00
Aaron Enye Shi 914506055e Update hip-math-api doc to remove non-default-rounded
[ROCm/hip commit: 7223277aa3]
2018-11-05 22:54:55 +00:00
Aaron Enye Shi 1c6f47ef55 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/hip commit: 2b108a2cfd]
2018-11-05 22:34:16 +00:00
Maneesh Gupta 2020c337c2 Merge pull request #747 from scchan/fix_hip_malloc_global_arrays
Move the global arrays for hip malloc/free

[ROCm/hip commit: f033d82072]
2018-11-02 11:32:11 +05:30
Alex Voicu 9cd4a9dbb1 Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_get_alignment_and_size_from_metadata
[ROCm/hip commit: f28cde3f98]
2018-11-01 23:17:27 +00:00
Siu Chi Chan 1159b4aa05 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/hip commit: 0ff408a56c]
2018-11-01 16:20:35 -04:00
Evgeny Mankov fc3076badf Merge pull request #746 from emankov/master
[HIPIFY][doc] Update README.md

[ROCm/hip commit: df2dd762c2]
2018-11-01 19:13:22 +03:00
Evgeny Mankov 4dd080b3d0 [HIPIFY][doc] Update README.md
+ Split Linux and Windows sections
+ Rewrite Testing section


[ROCm/hip commit: 9f1666e37a]
2018-11-01 19:11:40 +03:00
Evgeny Mankov 5c45c13b54 Merge pull request #745 from emankov/master
[HIPIFY][fix] Fix typo and functions' string arguments

[ROCm/hip commit: 63522c329b]
2018-11-01 17:03:01 +03:00
Evgeny Mankov 883f902eaf [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/hip commit: eff5d3fc1b]
2018-11-01 16:57:57 +03:00
Maneesh Gupta 2031beba9c Merge pull request #744 from mangupta/hipfuncattrib
typedef struct hipFuncAttributes now C compatible.

[ROCm/hip commit: 1c093592fa]
2018-10-31 16:25:25 +05:30
Jeff Daily c28043bc4f typedef struct hipFuncAttributes now C compatible.
Fixes #591.
Fixes #694.


[ROCm/hip commit: bb447dd76e]
2018-10-31 14:12:45 +05:30
Maneesh Gupta d17d335d6f 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/hip commit: 9199fe21dd]
2018-10-31 14:08:58 +05:30
Maneesh Gupta ac071f5390 Merge pull request #714 from aaronenyeshi/remove-static-hip-device
Remove libhip_device.a static library

[ROCm/hip commit: 0b86b421c1]
2018-10-31 14:08:29 +05:30
Maneesh Gupta 3986e47f8d Merge pull request #713 from scchan/master-hcc_early_finalize_support
Support more than one device code blobs in a single .kernel section

[ROCm/hip commit: 7f3e7b5334]
2018-10-31 14:04:06 +05:30
Alex Voicu 726b654c6d Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_get_alignment_and_size_from_metadata
[ROCm/hip commit: d035cb9000]
2018-10-30 23:34:46 +00:00
Alex Voicu d3beba42d3 If we've already seen a __global__ function we do not need to re-parse
[ROCm/hip commit: f7ba987038]
2018-10-30 23:34:27 +00:00
Rahul Garg d4815f4178 Fixes global symbols tracking in hip_module
[ROCm/hip commit: b270313129]
2018-10-31 03:22:38 +05:30
Evgeny Mankov 5e771d2c4f Merge pull request #741 from emankov/master
[HIPIFY][fix][#739] Fix garbage after replacements

[ROCm/hip commit: e17d24b46f]
2018-10-30 19:37:19 +03:00
Evgeny Mankov 96fefc34b4 [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/hip commit: a8e6033aa3]
2018-10-30 19:35:59 +03:00
Evgeny Mankov d8c4c3f940 Merge pull request #740 from emankov/master
[HIPIFY][fix] Return back cudaDeviceProp's struct field warpSize to hipWarpSize mapping

[ROCm/hip commit: ce2a7b849f]
2018-10-30 15:55:17 +03:00
Evgeny Mankov e4d356fdae [HIPIFY][fix] Return back cudaDeviceProp's struct field warpSize to hipWarpSize mapping.
[ROCm/hip commit: 104be4b677]
2018-10-30 15:53:00 +03:00
Maneesh Gupta fd748a8dd1 Merge pull request #726 from ROCm-Developer-Tools/feature_minimal_changes_for_hc_next
hipLaunchKernel, hipLaunchParm are deprecated, and shall be removed.

[ROCm/hip commit: 2c99ef9aee]
2018-10-30 09:20:39 +05:30