9899d0523e
hip-clang: Add __align__
...
CUDA has __align__. Define eqivalent for hip-clang.
[ROCm/hip commit: b9f8f977fb
2019-04-10 14:17:18 -04:00
72c1c756eb
Merge pull request #1015 from emankov/master
...
[HIPIFY] CUDA 10.1 Runtime API support
[ROCm/hip commit: 5732b74fc5
2019-04-10 18:44:21 +03:00
9087c06f8f
[HIPIFY] CUDA 10.1 Runtime API support
...
[ROCm/hip commit: d2d2889bfe
2019-04-10 18:41:36 +03:00
8fcd4075c0
Merge pull request #1014 from emankov/master
...
[HIPIFY] CUDA 10.1 Driver API support
[ROCm/hip commit: 472f7dfd19
2019-04-10 15:05:28 +03:00
ac64c184fb
[HIPIFY] CUDA 10.1 Driver API support
...
[ROCm/hip commit: b0879cd959
2019-04-10 15:03:34 +03:00
ae6c61575e
Merge pull request #1013 from yxsamliu/config
...
Fix hip-config.cmake for hip-clang
[ROCm/hip commit: fa6ba987a5
2019-04-10 07:53:22 +00:00
4f80c4d0f6
Merge pull request #1012 from yxsamliu/header
...
hip-clang: add include path for hsa headers
[ROCm/hip commit: ca827e8196
2019-04-10 07:53:13 +00:00
cc4acbdd08
hip-clang: fix hipcc options
...
Use -O3 for default optimization level.
Fix --hip-device-lib-path for warnings about unused option.
[ROCm/hip commit: a31036ab74
2019-04-09 22:31:13 -04:00
a38f40a151
Fix hip-config.cmake for hip-clang
...
Define HIP_COMPILER and HIP_RUNTIME in hip-config.cmake to
facilitate other packages identify hip-clang and HIP/VDI
runtime.
[ROCm/hip commit: cce99bfa24
2019-04-09 16:41:01 -04:00
0f62034e00
hip-clang: add include path for hsa headers
...
[ROCm/hip commit: c0e0ea9a12
2019-04-09 15:01:50 -04:00
8e683f7e57
Merge 'master' into 'amd-master'
...
Change-Id: Ib0feeb627038de9dcff12beb1386a2ff3d9524ec
[ROCm/hip commit: d099d37c72
2019-04-09 04:09:45 -05:00
a863c0dbee
Merge pull request #1010 from ROCm-Developer-Tools/mangupta-patch-1
...
[ci] Disable hipLaunchParm.tst for now
[ROCm/hip commit: 035a3e5aa2
2019-04-09 03:19:56 +00:00
3fe8efd799
Merge pull request #1011 from emankov/master
...
[HIPIFY][cmake][doc] Update CMakeLists and Readme cause CUDA 10.1 and clang 8.0.0 are released
[ROCm/hip commit: 1616929d37
2019-04-08 20:10:32 +03:00
cb90b40344
[HIPIFY][cmake][doc] Update CMakeLists and Readme cause CUDA 10.1 and clang 8.0.0 are released
...
+ Fix the error in cmake: clang 8.0.0 supports CUDA 10.0, not 10.1; only trunk clang 9.0.0 supports CUDA 10.1.
+ Update Readme:
1. clang's bug 36384 is gone, so latest stable release for Linux is clang 8.0.0, which supports CUDA up to 10.0;
2. update dependencies, testing and building notes.
[ROCm/hip commit: 53091e5378
2019-04-08 20:05:21 +03:00
eabfd4c6f4
[ci] Disable hipLaunchParm.tst for now
...
Due to a HCC bug in rocm-head, the test fails to compile. Disabling the test until the issue is resolved.
Change-Id: Ib4e7baf0b9c2cb5f5dbe38e6dd2bab894d28886a
[ROCm/hip commit: 0a52c6661d
2019-04-08 16:14:25 +05:30
c692428e15
Merge 'master' into 'amd-master'
...
Change-Id: Iac8fdc129d1c7b48c445afdaf09bd83a337185cf
[ROCm/hip commit: 3c92e2da24
2019-04-08 04:09:39 -05:00
d51941ac41
Merge pull request #1009 from yxsamliu/fix-mgpu
...
Fix regression on multi-gpu due to PR#997
[ROCm/hip commit: df09d42392
2019-04-08 08:20:17 +00:00
cf4bdb8b55
Fix regression on multi-gpu due to PR#997
...
[ROCm/hip commit: 271fdc4e4d
2019-04-05 22:54:41 -04:00
be808fd3ca
Merge pull request #1003 from acowley/patch-1
...
hipify: translate cudaErrorInvalidSymbol
[ROCm/hip commit: 25bb74a2bb
2019-04-05 20:21:27 +03:00
372417b923
Merge pull request #1007 from emankov/master
...
[HIP][doc] Fix typos and minor text inaccuracies in HIP FAQ
[ROCm/hip commit: dc7f7d14c7
2019-04-05 20:18:01 +03:00
ee887dd6a2
append the ELF flags for sram-ecc and xnack to the target triple per code object
...
[ROCm/hip commit: c61f265657
2019-04-05 13:17:11 -04:00
93433d9fe1
[HIPIFY][doc] Fix typos and minor text inaccuracies in HIP FAQ
...
[ROCm/hip commit: 6e70b8494b
2019-04-05 19:19:38 +03:00
23df3b5879
minor workaround for lazy binding
...
[ROCm/hip commit: e126f7254c
2019-04-02 17:28:06 -04:00
7a5276ca35
Merge 'master' into 'amd-master'
...
Change-Id: I4369829444ebd150e59f07f5db44e4584d9cc396
[ROCm/hip commit: 87ce7c278a
2019-04-02 12:33:16 -05:00
b00a98f27a
hipify: translate cudaErrorInvalidSymbol
...
[ROCm/hip commit: e9b1881c60
2019-04-02 08:54:37 -04:00
8a93d8e9aa
Merge pull request #998 from yxsamliu/doc
...
hip-clang: update installation guide.
[ROCm/hip commit: c19874e0f1
2019-04-02 05:08:18 +00:00
1fbff012b4
Merge pull request #997 from yxsamliu/mgpu
...
hip-clang: fix kernel not found on multi-gpu
[ROCm/hip commit: 5b1e63ee2d
2019-04-02 05:07:31 +00:00
772b4978ed
Merge pull request #1001 from emankov/master
...
[HIPIFY][tests] Fix typo in test for CUDA 10.x
[ROCm/hip commit: 9f40e0aa97
2019-04-01 19:53:42 +03:00
7bbf825c74
[HIPIFY][tests] Fix typo in test for CUDA 10.x
...
[ROCm/hip commit: 8bca9f1d7a
2019-04-01 19:52:08 +03:00
3b28e2f9b4
Merge pull request #1000 from emankov/master
...
[HIPIFY][cmake] Update CMakeLists and Readme cause CUDA 10.1 and clang 8.0.0 are released
[ROCm/hip commit: a7d0e40058
2019-04-01 19:49:46 +03:00
9e32584753
[HIPIFY][cmake] Update CMakeLists and Readme cause CUDA 10.1 and clang 8.0.0 are released
...
[ROCm/hip commit: 7c221450fa
2019-04-01 19:44:52 +03:00
5072c98f32
hip-clang: fix kernel not found on multi-gpu
...
__hipRegisterFunction is called during by .init functions during program initialization.
It calls hipModuleGetFunction to locate kernel symbol in code objects. hipModuleGetFunction
assumes current device when locating kernel symbols. This works for HCC but not for hip-clang,
since hip-clang needs to locate kernel symbols for different devices without switching
between devices.
This patch introduces a new hsa agent parameter to ihipModuleGetFunction, which allows
__hipRegisterFunction to choose the correct hsa agent when locating kernel symbols. By
default it uses this_agent(), therefore this patch has no impact on HCC.
[ROCm/hip commit: 98b9e92908
2019-03-31 10:08:20 -04:00
595d95cfe8
Update INSTALL.md
...
[ROCm/hip commit: ed2fbb27e4
2019-03-30 08:29:08 -04:00
c0682dda96
hip-clang: update installation guide.
...
[ROCm/hip commit: 409aa49218
2019-03-30 08:24:49 -04:00
6218c5c00d
Merge 'master' into 'amd-master'
...
Change-Id: Id0b95bac00a76909d68f53406875028fdbb97ac7
[ROCm/hip commit: f0708722a3
2019-03-29 04:09:52 -05:00
1cc94f9369
Make hipModuleGetGlobal be in HIP runtime so it can be discovered at runtime ( #981 )
...
* Make hipModuleGetGlobal be in HIP runtime so it can be discovered at runtime
In HIP PR #929 , quite a few HIP public APIs were made as inline functions with
hidden visibility. It was necessary to support applications with shared
libraries with GPU kernels launched via hipLaunchKernelGGL(), after HIP runtime
is initialized.
In empirical tests, the implementation has been proved to be a bit too
excessive, especially for hipModuleGetGlobal(). The function is used by another
type of client applications which relies on the existence of this function
within HIP runtime so global symbols from HSA code objects loaded dynamically
at runtime can be retrieved programmtically.
This commit moves hipModuleGetGlobal() back to src/hip_module.cpp, and makes it
visible and not inline, to fulfill requirements for applications
aforementioned. It does not change the behavior of applications depending on
hipLaunchKernelGGL().
* Add HIP_INIT_API into the implementation of hipModuleGetGlobal
Address review comments.
* Fix failing HIP unit tests
[ROCm/hip commit: 4b7177ac42
2019-03-29 03:45:04 +00:00
f63c4be10e
Merge pull request #992 from gargrahul/handle_d2d_memcpy2d
...
Handle D2D in memcpy2D
[ROCm/hip commit: d0e5fbeb72
2019-03-28 04:41:36 +00:00
6effbfe2dd
Merge pull request #991 from jeffdaily/per_agent_program_state
...
load program state once per agent
[ROCm/hip commit: 8af327e439
2019-03-28 04:40:46 +00:00
fb2beb0c88
improve program state commentary
...
Disambiguate calling many varibles "agent".
More detail in exception message.
Create and discard map placeholders; no need to call std::vector::clear() on map value.
[ROCm/hip commit: 7aada87cbd
2019-03-27 21:40:27 +00:00
0eaa29ad06
Handle D2D in memcpy2D
...
[ROCm/hip commit: 0c55db8552
2019-03-28 02:21:45 +05:30
21f5e142f5
load program state once per agent
...
[ROCm/hip commit: c9117de8eb
2019-03-27 18:19:10 +00:00
0961cb0eee
Merge 'master' into 'amd-master'
...
Change-Id: Id7c377bd22abccbdffd9d1f8bd31a482102813ce
[ROCm/hip commit: e21df30587
2019-03-27 04:09:48 -05:00
87772a479e
Merge pull request #987 from gargrahul/fix_hostmalloc_double_device_map
...
Avoid double mapping of devices to hostMalloc buffer
[ROCm/hip commit: 08e12e730e
2019-03-27 05:23:47 +00:00
464c023bb5
Merge pull request #990 from mhbliao/hliao/master/sw
...
SWDEV-184380 Fix hcc compilation
[ROCm/hip commit: e66dfa6ea3
2019-03-27 05:23:26 +00:00
ed99892664
Merge pull request #986 from mhbliao/hliao/master/build
...
[hip] Fix typo in macro `hipLaunchKernel`
[ROCm/hip commit: 3535ced23f
2019-03-27 05:22:44 +00:00
a9a397bc4b
SWDEV-184380 Fix hcc compilation
...
- `hcc` has no builtin. Need to invoke LLVM intrinsic directly.
[ROCm/hip commit: 939d153c1a
2019-03-26 15:20:17 -04:00
d98d5ca12a
Let hipHostMalloc always share/map pinned host ptr
...
[ROCm/hip commit: f0af073793
2019-03-26 10:19:13 +05:30
c6ef785464
Avoid double mapping of devices to hostMalloc buffer
...
[ROCm/hip commit: 5e917d70f3
2019-03-25 23:07:05 +05:30
94b7856a1a
[hip] Fix typo in macro hipLaunchKernel
...
[ROCm/hip commit: b3497824ec
2019-03-25 12:06:46 -04:00
5967d30f6f
Merge 'master' into 'amd-master'
...
Change-Id: I759c530530011ee9cff5aef00944c190e4204df2
[ROCm/hip commit: 0573395340
2019-03-25 09:17:20 -05:00
Yaxun (Sam) Liu
Evgeny Mankov
Maneesh Gupta
Jenkins
David Salinas
Siu Chi Chan
Anthony Cowley
Wen-Heng (Jack) Chung
Jeff Daily
Rahul Garg
Michael LIAO