63e926cec7
2D Fallback needs hcc workweek 19101 or higher
...
[ROCm/hip commit: 9bbfbceb64
2019-03-25 12:07:28 +05:30
a3fb908a0a
Add 2D fallback to use copy kernel
...
[ROCm/hip commit: 918d7e3a40
2019-03-14 13:03:06 +05:30
3f5e937afc
Merge pull request #949 from gargrahul/single_stream_concurrent_kernels
...
Add extension for kernel concurrency on same stream
[ROCm/hip commit: 352b17346c
2019-03-06 17:34:54 +05:30
0c16497abd
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.
[ROCm/hip commit: ea0fcf3e61
2019-03-06 17:31:44 +05:30
5d6fd17fbe
Add extension for kernel concurrency on same stream
...
[ROCm/hip commit: 59081c69fc
2019-03-06 12:55:39 +05:30
da589e38ed
Address code review comments to use hipDeviceptr_t
...
[ROCm/hip commit: 5cbd28f29b
2019-03-05 05:51:05 +00:00
0b7f38d100
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
[ROCm/hip commit: 7ebbbd3525
2019-03-04 17:00:33 +00:00
4a0d68ba3f
Fix hipMemset3D test
...
Calculate the allocated size based on the width, height and depth.
[ROCm/hip commit: 8d92d1ebd7
2019-02-28 22:42:46 +00:00
7ef8b1138f
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.
[ROCm/hip commit: c5e813f64c
2019-02-21 12:48:28 -05:00
a9d82ed57b
Merge pull request #899 from lmoriche/hip_clang
...
Add code-object-v3 support for the HIP-Clang path.
[ROCm/hip commit: 005e09f5b9
2019-02-06 19:50:51 -08:00
1bbb9d455b
Add code-object-v3 support for the HIP-Clang path.
...
[ROCm/hip commit: 6ab8711f02
2019-02-05 14:43:26 -08:00
089077a8b7
Revert "Fixed issue of GPU device losing access to host pinned memory"
...
[ROCm/hip commit: 3120db15e4
2019-02-04 22:45:13 -08:00
7aafa0da9f
Fixed issue of GPU device losing access to host pinned memory
...
[ROCm/hip commit: bab3a94b33
2019-01-22 06:25:43 +05:30
3f7ff3450e
fixing HSA_INIT_API cid args
...
[ROCm/hip commit: 0164464bcc
2019-01-16 23:45:44 -06:00
e2911291dd
Ensure that static structures are populated
...
[ROCm/hip commit: 0b57f50855
2019-01-09 17:21:53 +00:00
2f9021afd3
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.
[ROCm/hip commit: b4d658a48f
2019-01-08 17:33:40 +00:00
587745b841
Hook into the creaky lazy-reinit machinery. Try to minimise race-risk.
...
[ROCm/hip commit: ec14daa7ce
2019-01-01 11:01:16 +05:30
e127990e23
More blobs, more problems.
...
[ROCm/hip commit: 340674ceb6
2019-01-01 11:01:07 +05:30
7bcb83a05f
Start re-working 731 for 2.0.
...
[ROCm/hip commit: 25c7e5d609
2019-01-01 11:00:57 +05:30
3cf96f31d0
Merge pull request #797 from gargrahul/fixhipPointerGetAttributes
...
Fixed hipPointerGetAttributes for hostmalloced ptr
[ROCm/hip commit: 56ce3e37d5
2018-12-12 10:16:07 +05:30
07dcdff9e5
Merge pull request #608 from gargrahul/add_pinned_2d_sdma_copy
...
Added support for pinned 2D SDMA copy
[ROCm/hip commit: 0dd26b4f63
2018-12-12 07:44:16 +05:30
b304ff5210
Fixed hipPointerGetAttributes for hostmalloced ptr
...
[ROCm/hip commit: 5f12067708
2018-12-08 01:42:08 +05:30
bca8022aa0
Revert "Rely on code object metadat for kernarg arguments alignof and sizeof."
...
This reverts commit 6d64f5e1121fbf639962
2018-11-29 11:38:37 -05:00
a72a54996e
Revert "Handle the very confusing dual encoding of the symbol name."
...
This reverts commit 2a69dd1fb671189c10c1
2018-11-29 11:38:36 -05:00
8bf51361e4
Revert "If we've already seen a __global__ function we do not need to re-parse"
...
This reverts commit d3beba42d309f87e41d9
2018-11-29 11:38:35 -05:00
a715dea79c
Revert "Missing handling nullary __global__ functions for mixed arity cases."
...
This reverts commit 51c47fcc2e8eb9b38e76
2018-11-29 11:38:31 -05:00
954535e0b5
Revert "Fix issue in kernarg metadata parsing due to early finalization"
...
This reverts commit 48c2d69d32909609773c
2018-11-29 11:35:00 -05:00
95802a836b
Let hip-clang support --genco
...
[ROCm/hip commit: 450f093231
2018-11-27 15:55:50 -05:00
28c52ae091
Merge pull request #772 from scchan/kernarg_metadata_early_finalize
...
Fix issue in kernarg metadata parsing due to early finalization
[ROCm/hip commit: 9a1d8137eb
2018-11-26 08:55:19 +05:30
e317a9a1fa
Merge pull request #773 from fronteer/master
...
Support of printing process ID for HIP tracing
[ROCm/hip commit: 7ce082415b
2018-11-23 11:16:22 +05:30
05e09614be
Merge pull request #760 from eshcherb/roctracer-hip-frontend-181113
...
Roctracer hip frontend 181113
[ROCm/hip commit: 160c509e23
2018-11-23 11:08:25 +05:30
724a1e6dc5
Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP
...
[ROCm/hip commit: 91e8ec9e4b
2018-11-22 19:11:49 +08:00
26b7fef858
Add support of printing process ID for HIP Tracing
...
[ROCm/hip commit: 81cf7cabfa
2018-11-22 18:58:06 +08:00
48c2d69d32
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
[ROCm/hip commit: 19acf86cef
2018-11-21 12:09:46 -05:00
e2bc3e49a5
Merge pull request #748 from mkuron/getsymboladdress
...
Implement hipGetSymbolAddress and hipGetSymbolSize
[ROCm/hip commit: bcea027bf1
2018-11-21 10:32:01 +05:30
c35dfb71d5
Merge branch 'master' into getsymboladdress
...
[ROCm/hip commit: 8610128c3e
2018-11-20 12:03:22 +01:00
89efed29d7
Fix hipHostRegister
...
[ROCm/hip commit: 1a038879a9
2018-11-17 05:38:35 +05:30
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
dbc30b7800
rebase to master, tracer related changes
...
[ROCm/hip commit: 091124a766
2018-11-13 15:50:34 +00:00
73e3c4ec42
renaming HIP_INIT_CB_API to HIP_INIT_API
...
[ROCm/hip commit: e5ba097afd
2018-11-13 15:33:26 +00:00
7f6832cbe5
hip_prof_(api/str).h moving under hcc_detail dir
...
[ROCm/hip commit: 47f1d059d1
2018-11-13 15:33:26 +00:00
c6dbcf8d48
adding lost i the merge change
...
[ROCm/hip commit: cba2d42bbf
2018-11-13 15:33:26 +00:00
0a58dc9b7b
adding activity prof layer
...
[ROCm/hip commit: b8b1637ef7
2018-11-13 15:33:26 +00:00
30c4fd3875
Fixed symbol tracking device index
...
[ROCm/hip commit: 6b3cbc65ad
2018-11-13 07:01:17 +05:30
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
51c47fcc2e
Missing handling nullary __global__ functions for mixed arity cases.
...
[ROCm/hip commit: 4ebc229b9a
2018-11-12 01:51:59 +00:00
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
aaf12143ae
Add more checks for fatbin
...
[ROCm/hip commit: a31b6b78d5
2018-11-08 16:46:01 -05:00
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
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
Rahul Garg
Maneesh Gupta
Alex Voicu
Wen-Heng (Jack) Chung
Wilkin Chau
Yaxun Sam Liu
lmoriche
Laurent Morichetti
Rahul Garg
Evgeny
Siu Chi Chan
Qianfeng Zhang
Michael Kuron
root