6fa50a2e79
Merge 'master' into 'amd-master'
...
Change-Id: I79fc1a5d5692ae9783b9e26c7adecc6c707da977
[ROCm/clr commit: 81d46ce8ac
2019-04-11 10:42:54 -05:00
4610845721
Merge pull request #1016 from yxsamliu/align
...
hip-clang: Add __align__
[ROCm/clr commit: 464e098796
2019-04-11 08:54:23 +05:30
c35dfe9cfa
Merge 'master' into 'amd-master'
...
Change-Id: I0e895e45f3a2159dc032a269c5706ed7246857ea
[ROCm/clr commit: 0a3ffdf182
2019-04-10 16:37:43 -05:00
7d58d7b02a
hip-clang: Add __align__
...
CUDA has __align__. Define eqivalent for hip-clang.
[ROCm/clr commit: e200ece4da
2019-04-10 14:17:18 -04:00
19ba784652
Merge pull request #1015 from emankov/master
...
[HIPIFY] CUDA 10.1 Runtime API support
[ROCm/clr commit: 131e74c64c
2019-04-10 18:44:21 +03:00
ca6021640b
[HIPIFY] CUDA 10.1 Runtime API support
...
[ROCm/clr commit: b11bf48270
2019-04-10 18:41:36 +03:00
971a55a94a
Merge pull request #1014 from emankov/master
...
[HIPIFY] CUDA 10.1 Driver API support
[ROCm/clr commit: 2603fb409b
2019-04-10 15:05:28 +03:00
61a6949cf0
[HIPIFY] CUDA 10.1 Driver API support
...
[ROCm/clr commit: 9a660c0d48
2019-04-10 15:03:34 +03:00
f8194fd6f1
Merge pull request #1013 from yxsamliu/config
...
Fix hip-config.cmake for hip-clang
[ROCm/clr commit: 75691ff3e4
2019-04-10 07:53:22 +00:00
95218deb30
Merge pull request #1012 from yxsamliu/header
...
hip-clang: add include path for hsa headers
[ROCm/clr commit: 9a1f5c99fc
2019-04-10 07:53:13 +00:00
f6151a55fd
hip-clang: fix hipcc options
...
Use -O3 for default optimization level.
Fix --hip-device-lib-path for warnings about unused option.
[ROCm/clr commit: 419eeb4fe0
2019-04-09 22:31:13 -04:00
65aa1eb59c
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/clr commit: a781d2e017
2019-04-09 16:41:01 -04:00
40cf556b82
hip-clang: add include path for hsa headers
...
[ROCm/clr commit: 98642129cc
2019-04-09 15:01:50 -04:00
ec521bee59
Merge 'master' into 'amd-master'
...
Change-Id: Ib0feeb627038de9dcff12beb1386a2ff3d9524ec
[ROCm/clr commit: 82810ecc0d
2019-04-09 04:09:45 -05:00
6f8a83bd11
Merge pull request #1010 from ROCm-Developer-Tools/mangupta-patch-1
...
[ci] Disable hipLaunchParm.tst for now
[ROCm/clr commit: aa8f17193e
2019-04-09 03:19:56 +00:00
ea4138430e
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/clr commit: 18b3cbbb4c
2019-04-08 20:10:32 +03:00
0947324f18
[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/clr commit: 79e6bd8426
2019-04-08 20:05:21 +03:00
47fab26a20
[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/clr commit: 27013c9af6
2019-04-08 16:14:25 +05:30
5f649d81eb
Merge 'master' into 'amd-master'
...
Change-Id: Iac8fdc129d1c7b48c445afdaf09bd83a337185cf
[ROCm/clr commit: 52b469b6e0
2019-04-08 04:09:39 -05:00
dfb2a26ad9
Merge pull request #1009 from yxsamliu/fix-mgpu
...
Fix regression on multi-gpu due to PR#997
[ROCm/clr commit: 6b47979b8a
2019-04-08 08:20:17 +00:00
d8acabf24c
Fix regression on multi-gpu due to PR#997
...
[ROCm/clr commit: 5c67ee11f4
2019-04-05 22:54:41 -04:00
8d78207849
Merge pull request #1003 from acowley/patch-1
...
hipify: translate cudaErrorInvalidSymbol
[ROCm/clr commit: 3352d7b174
2019-04-05 20:21:27 +03:00
93be84247c
Merge pull request #1007 from emankov/master
...
[HIP][doc] Fix typos and minor text inaccuracies in HIP FAQ
[ROCm/clr commit: 90225d2a39
2019-04-05 20:18:01 +03:00
9eb10c5b4d
[HIPIFY][doc] Fix typos and minor text inaccuracies in HIP FAQ
...
[ROCm/clr commit: 4990a1003b
2019-04-05 19:19:38 +03:00
8b22d2b1f6
Merge 'master' into 'amd-master'
...
Change-Id: I4369829444ebd150e59f07f5db44e4584d9cc396
[ROCm/clr commit: 5a6d260117
2019-04-02 12:33:16 -05:00
191dfc8dff
hipify: translate cudaErrorInvalidSymbol
...
[ROCm/clr commit: f15dd58a91
2019-04-02 08:54:37 -04:00
bedff2406a
Merge pull request #998 from yxsamliu/doc
...
hip-clang: update installation guide.
[ROCm/clr commit: 2d9e5615b7
2019-04-02 05:08:18 +00:00
9d2c0c8e5d
Merge pull request #997 from yxsamliu/mgpu
...
hip-clang: fix kernel not found on multi-gpu
[ROCm/clr commit: a6e7dfefe3
2019-04-02 05:07:31 +00:00
1168e2925b
Merge pull request #1001 from emankov/master
...
[HIPIFY][tests] Fix typo in test for CUDA 10.x
[ROCm/clr commit: 887c096ed7
2019-04-01 19:53:42 +03:00
17ac0d3e19
[HIPIFY][tests] Fix typo in test for CUDA 10.x
...
[ROCm/clr commit: 5b59f87305
2019-04-01 19:52:08 +03:00
7d93455770
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/clr commit: 16128da4a3
2019-04-01 19:49:46 +03:00
236624a229
[HIPIFY][cmake] Update CMakeLists and Readme cause CUDA 10.1 and clang 8.0.0 are released
...
[ROCm/clr commit: 799a6f5512
2019-04-01 19:44:52 +03:00
12ac74bad1
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/clr commit: 8f5c812a68
2019-03-31 10:08:20 -04:00
54c2b79351
Update INSTALL.md
...
[ROCm/clr commit: 76a9fdd924
2019-03-30 08:29:08 -04:00
79ac0097dc
hip-clang: update installation guide.
...
[ROCm/clr commit: 598604aa7f
2019-03-30 08:24:49 -04:00
d02a41f291
Merge 'master' into 'amd-master'
...
Change-Id: Id0b95bac00a76909d68f53406875028fdbb97ac7
[ROCm/clr commit: 45c92008c1
2019-03-29 04:09:52 -05:00
cfe930f9d6
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/clr commit: 04915cea2f
2019-03-29 03:45:04 +00:00
d99bc4c540
Merge pull request #992 from gargrahul/handle_d2d_memcpy2d
...
Handle D2D in memcpy2D
[ROCm/clr commit: f9f4cee347
2019-03-28 04:41:36 +00:00
a2191a80a6
Merge pull request #991 from jeffdaily/per_agent_program_state
...
load program state once per agent
[ROCm/clr commit: 79f24a1553
2019-03-28 04:40:46 +00:00
5233d41c6c
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/clr commit: f5e4fff6cc
2019-03-27 21:40:27 +00:00
73bb9a74bb
Handle D2D in memcpy2D
...
[ROCm/clr commit: 50d623981e
2019-03-28 02:21:45 +05:30
9cee2c5311
load program state once per agent
...
[ROCm/clr commit: 2845b4c4b8
2019-03-27 18:19:10 +00:00
6f87eff3aa
Merge 'master' into 'amd-master'
...
Change-Id: Id7c377bd22abccbdffd9d1f8bd31a482102813ce
[ROCm/clr commit: 4d25945c7d
2019-03-27 04:09:48 -05:00
a0b29c8ed0
Merge pull request #987 from gargrahul/fix_hostmalloc_double_device_map
...
Avoid double mapping of devices to hostMalloc buffer
[ROCm/clr commit: 93906a072c
2019-03-27 05:23:47 +00:00
6fb7f626ba
Merge pull request #990 from mhbliao/hliao/master/sw
...
SWDEV-184380 Fix hcc compilation
[ROCm/clr commit: 178e3ecdca
2019-03-27 05:23:26 +00:00
80543778a3
Merge pull request #986 from mhbliao/hliao/master/build
...
[hip] Fix typo in macro `hipLaunchKernel`
[ROCm/clr commit: 3bcb3a9239
2019-03-27 05:22:44 +00:00
c5717a37d7
SWDEV-184380 Fix hcc compilation
...
- `hcc` has no builtin. Need to invoke LLVM intrinsic directly.
[ROCm/clr commit: d355122bf9
2019-03-26 15:20:17 -04:00
0d47ae4203
Let hipHostMalloc always share/map pinned host ptr
...
[ROCm/clr commit: 9b38380c03
2019-03-26 10:19:13 +05:30
21d7bbab11
Avoid double mapping of devices to hostMalloc buffer
...
[ROCm/clr commit: ad11972f47
2019-03-25 23:07:05 +05:30
5482fa8102
[hip] Fix typo in macro hipLaunchKernel
...
[ROCm/clr commit: 13655df76e
2019-03-25 12:06:46 -04:00
Jenkins
Maneesh Gupta
Yaxun (Sam) Liu
Evgeny Mankov
Anthony Cowley
Wen-Heng (Jack) Chung
Jeff Daily
Rahul Garg
Michael LIAO