352b17346c
Merge pull request #949 from gargrahul/single_stream_concurrent_kernels
...
Add extension for kernel concurrency on same stream
2019-03-06 17:34:54 +05:30
ea0fcf3e61
dlopen() fixes ( #929 )
...
* Initial attempt to switch over to internally linked state.
* Add missing CMake update.
* hipLaunchKernelGGLImpl must be inline as well. Ensure internal linkage.
* Ensure global retrieval uses internally linked state.
* Hide HC in the implementation. Minimise ADL woes.
* Strange software exists, and must be catered to.
* Use a less spammy mechanism for ensuring internal linkage / non-export.
* Remove leftover internal detail.
2019-03-06 17:31:44 +05:30
59081c69fc
Add extension for kernel concurrency on same stream
2019-03-06 12:55:39 +05:30
5cbd28f29b
Address code review comments to use hipDeviceptr_t
2019-03-05 05:51:05 +00:00
7ebbbd3525
Add hipMemsetD32 and hipMemsetD32Async
...
Add 2 extra memset functions which fills memory with integer-typed data
Also change the parameters of ihipMemset to better explain the semantic
2019-03-04 17:00:33 +00:00
8d92d1ebd7
Fix hipMemset3D test
...
Calculate the allocated size based on the width, height and depth.
2019-02-28 22:42:46 +00:00
c5e813f64c
Add __gnu_h2f_ieee and __gnu_f2h_ieee
...
The implementation is copied from HCC runtime.
For hcc it has no effect since apps can find them in either hcc runtime or HIP
runtime.
hip-clang needs it in HIP/HCC runtime so that HIP/HCC and HIP/VDI runtime are
swappable.
2019-02-21 12:48:28 -05:00
005e09f5b9
Merge pull request #899 from lmoriche/hip_clang
...
Add code-object-v3 support for the HIP-Clang path.
2019-02-06 19:50:51 -08:00
6ab8711f02
Add code-object-v3 support for the HIP-Clang path.
2019-02-05 14:43:26 -08:00
3120db15e4
Revert "Fixed issue of GPU device losing access to host pinned memory"
2019-02-04 22:45:13 -08:00
bab3a94b33
Fixed issue of GPU device losing access to host pinned memory
2019-01-22 06:25:43 +05:30
0164464bcc
fixing HSA_INIT_API cid args
2019-01-16 23:45:44 -06:00
0b57f50855
Ensure that static structures are populated
2019-01-09 17:21:53 +00:00
b4d658a48f
Introduce hash key to HIP module implementation
...
A hash calculated via FNV-1a algorithm is introduced in ihipModule_t, the
internal of hipModule_t. The hash is used by HIP module APIs such as
- read_agent_global_from_module
to determine whether the agent-scope globals for a module have been iterated.
This commit fixes one issue that applications which load / unload modules
frequently would occasionally fail. After deep investigation of the issue it
turns out the old implementation in read_agent_global_from_module uses
hipModule_t as the key, which is not robust enough, as hipModule_t instances
are allocated dynamically so there are cases that one memory address may be
used by multiple hipModule_t instances. The real solution is to introduce a
uniquely identifiable hash for the code object associated with the HIP module.
And that's the rationale behind this commit.
2019-01-08 17:33:40 +00:00
ec14daa7ce
Hook into the creaky lazy-reinit machinery. Try to minimise race-risk.
2019-01-01 11:01:16 +05:30
340674ceb6
More blobs, more problems.
2019-01-01 11:01:07 +05:30
25c7e5d609
Start re-working 731 for 2.0.
2019-01-01 11:00:57 +05:30
56ce3e37d5
Merge pull request #797 from gargrahul/fixhipPointerGetAttributes
...
Fixed hipPointerGetAttributes for hostmalloced ptr
2018-12-12 10:16:07 +05:30
0dd26b4f63
Merge pull request #608 from gargrahul/add_pinned_2d_sdma_copy
...
Added support for pinned 2D SDMA copy
2018-12-12 07:44:16 +05:30
5f12067708
Fixed hipPointerGetAttributes for hostmalloced ptr
2018-12-08 01:42:08 +05:30
1fbf639962
Revert "Rely on code object metadat for kernarg arguments alignof and sizeof."
...
This reverts commit fe1e963299
2018-11-29 11:38:37 -05:00
71189c10c1
Revert "Handle the very confusing dual encoding of the symbol name."
...
This reverts commit bce3de8162
2018-11-29 11:38:36 -05:00
09f87e41d9
Revert "If we've already seen a __global__ function we do not need to re-parse"
...
This reverts commit f7ba987038
2018-11-29 11:38:35 -05:00
8eb9b38e76
Revert "Missing handling nullary __global__ functions for mixed arity cases."
...
This reverts commit 4ebc229b9a
2018-11-29 11:38:31 -05:00
909609773c
Revert "Fix issue in kernarg metadata parsing due to early finalization"
...
This reverts commit 19acf86cef
2018-11-29 11:35:00 -05:00
450f093231
Let hip-clang support --genco
2018-11-27 15:55:50 -05:00
9a1d8137eb
Merge pull request #772 from scchan/kernarg_metadata_early_finalize
...
Fix issue in kernarg metadata parsing due to early finalization
2018-11-26 08:55:19 +05:30
7ce082415b
Merge pull request #773 from fronteer/master
...
Support of printing process ID for HIP tracing
2018-11-23 11:16:22 +05:30
160c509e23
Merge pull request #760 from eshcherb/roctracer-hip-frontend-181113
...
Roctracer hip frontend 181113
2018-11-23 11:08:25 +05:30
91e8ec9e4b
Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP
2018-11-22 19:11:49 +08:00
81cf7cabfa
Add support of printing process ID for HIP Tracing
2018-11-22 18:58:06 +08:00
19acf86cef
Fix issue in kernarg metadata parsing due to early finalization
...
The logic to parse the kernel metadata is unaware that enabling
of early finalization could result in multiple code blobs in a
single .kernel section. This teaches the HIP runtime to handle
that.
Change-Id: I1581b42f0da8b30233d7898014f7468728c1d489
2018-11-21 12:09:46 -05:00
bcea027bf1
Merge pull request #748 from mkuron/getsymboladdress
...
Implement hipGetSymbolAddress and hipGetSymbolSize
2018-11-21 10:32:01 +05:30
8610128c3e
Merge branch 'master' into getsymboladdress
2018-11-20 12:03:22 +01:00
1a038879a9
Fix hipHostRegister
2018-11-17 05:38:35 +05:30
b4e4aafc16
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
091124a766
rebase to master, tracer related changes
2018-11-13 15:50:34 +00:00
e5ba097afd
renaming HIP_INIT_CB_API to HIP_INIT_API
2018-11-13 15:33:26 +00:00
47f1d059d1
hip_prof_(api/str).h moving under hcc_detail dir
2018-11-13 15:33:26 +00:00
cba2d42bbf
adding lost i the merge change
2018-11-13 15:33:26 +00:00
b8b1637ef7
adding activity prof layer
2018-11-13 15:33:26 +00:00
6b3cbc65ad
Fixed symbol tracking device index
2018-11-13 07:01:17 +05:30
11e7ab8879
Fixed hipMemcpyToSymbol doesn't work on GPU other than device 0 SWDEV-166881
2018-11-13 00:49:20 +05:30
4ebc229b9a
Missing handling nullary __global__ functions for mixed arity cases.
2018-11-12 01:51:59 +00:00
eddb783e9b
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
a31b6b78d5
Add more checks for fatbin
2018-11-08 16:46:01 -05:00
aa6815cdc8
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
0a1584b075
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
e672dc8a55
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
8d8d12f65d
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
Alex Voicu
Rahul Garg
Wen-Heng (Jack) Chung
Wilkin Chau
Yaxun Sam Liu
lmoriche
Laurent Morichetti
Rahul Garg
Evgeny
Siu Chi Chan
Qianfeng Zhang
Michael Kuron
root