3955f2c131
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
ed48847237
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
263e82a67a
Add extension for kernel concurrency on same stream
2019-03-06 12:55:39 +05:30
8b7baa0bd9
Address code review comments to use hipDeviceptr_t
2019-03-05 05:51:05 +00:00
392271f4db
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
99540373cf
Fix hipMemset3D test
...
Calculate the allocated size based on the width, height and depth.
2019-02-28 22:42:46 +00:00
972ca06c4c
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
002bb4a94c
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
74578160bd
Add code-object-v3 support for the HIP-Clang path.
2019-02-05 14:43:26 -08:00
e94153ed8b
Revert "Fixed issue of GPU device losing access to host pinned memory"
2019-02-04 22:45:13 -08:00
f8b399d3b5
Fixed issue of GPU device losing access to host pinned memory
2019-01-22 06:25:43 +05:30
47625cb8fd
fixing HSA_INIT_API cid args
2019-01-16 23:45:44 -06:00
1c815170da
Ensure that static structures are populated
2019-01-09 17:21:53 +00:00
6e68d44220
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
3470692998
Hook into the creaky lazy-reinit machinery. Try to minimise race-risk.
2019-01-01 11:01:16 +05:30
b2f76123b1
More blobs, more problems.
2019-01-01 11:01:07 +05:30
3e8f198b58
Start re-working 731 for 2.0.
2019-01-01 11:00:57 +05:30
a778f7cdf7
Merge pull request #797 from gargrahul/fixhipPointerGetAttributes
...
Fixed hipPointerGetAttributes for hostmalloced ptr
2018-12-12 10:16:07 +05:30
6ce99b066c
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
77fd517e09
Fixed hipPointerGetAttributes for hostmalloced ptr
2018-12-08 01:42:08 +05:30
4251a70bc0
Revert "Rely on code object metadat for kernarg arguments alignof and sizeof."
...
This reverts commit 299b9d1382
2018-11-29 11:38:37 -05:00
a41bce5163
Revert "Handle the very confusing dual encoding of the symbol name."
...
This reverts commit 1fe33b4738
2018-11-29 11:38:36 -05:00
dc36c49212
Revert "If we've already seen a __global__ function we do not need to re-parse"
...
This reverts commit 1621deee71
2018-11-29 11:38:35 -05:00
c5df445d1f
Revert "Missing handling nullary __global__ functions for mixed arity cases."
...
This reverts commit 1e64813716
2018-11-29 11:38:31 -05:00
adbf0c444b
Revert "Fix issue in kernarg metadata parsing due to early finalization"
...
This reverts commit ba2b5ff9da
2018-11-29 11:35:00 -05:00
988dcd1e4a
Let hip-clang support --genco
2018-11-27 15:55:50 -05:00
3a41a8b1f1
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
5bfde06bcc
Merge pull request #773 from fronteer/master
...
Support of printing process ID for HIP tracing
2018-11-23 11:16:22 +05:30
99bb89b756
Merge pull request #760 from eshcherb/roctracer-hip-frontend-181113
...
Roctracer hip frontend 181113
2018-11-23 11:08:25 +05:30
4f85e98384
Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP
2018-11-22 19:11:49 +08:00
b88c8769ea
Add support of printing process ID for HIP Tracing
2018-11-22 18:58:06 +08:00
ba2b5ff9da
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
40d3184dd1
Merge pull request #748 from mkuron/getsymboladdress
...
Implement hipGetSymbolAddress and hipGetSymbolSize
2018-11-21 10:32:01 +05:30
e9b88711e2
Merge branch 'master' into getsymboladdress
2018-11-20 12:03:22 +01:00
aae87e21d2
Fix hipHostRegister
2018-11-17 05:38:35 +05:30
f769320b5c
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
0774b275c8
rebase to master, tracer related changes
2018-11-13 15:50:34 +00:00
e362688adf
renaming HIP_INIT_CB_API to HIP_INIT_API
2018-11-13 15:33:26 +00:00
8c88932f30
hip_prof_(api/str).h moving under hcc_detail dir
2018-11-13 15:33:26 +00:00
a13e035fd9
adding lost i the merge change
2018-11-13 15:33:26 +00:00
084a68be63
adding activity prof layer
2018-11-13 15:33:26 +00:00
70bb04cc61
Fixed symbol tracking device index
2018-11-13 07:01:17 +05:30
ac32566d9b
Fixed hipMemcpyToSymbol doesn't work on GPU other than device 0 SWDEV-166881
2018-11-13 00:49:20 +05:30
1e64813716
Missing handling nullary __global__ functions for mixed arity cases.
2018-11-12 01:51:59 +00:00
01ec23538e
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
80b382a37a
Add more checks for fatbin
2018-11-08 16:46:01 -05:00
392e2ba1ba
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
e510be9395
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
0bafc38135
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
8b1544c911
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