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
6ebcc2922c
Use correct trace macro in hipGetSymbolAddress/hipGetSymbolSize
2018-11-06 20:46:30 +01:00
31acf1c268
Introduce ihipModuleGetGlobal
2018-11-06 09:54:34 +01:00
73616582d6
Implement hipGetSymbolAddress and hipGetSymbolSize
2018-11-04 10:39:34 +01:00
f28cde3f98
Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_get_alignment_and_size_from_metadata
2018-11-01 23:17:27 +00:00
0ff408a56c
Move the global arrays for hip malloc/free
...
from a header into a source file such that
there's only an unique copy in an executable
and prevent wasting static memory on the host
Change-Id: Id5b62766f77809c8d7b47892cb7149c490dcbdb9
2018-11-01 16:20:35 -04:00
9199fe21dd
Merge pull request #733 from ex-rzr/fix_array_alloc_size
...
Fix allocation size of arrays with multiple and/or non-32-bit channels
2018-10-31 14:08:58 +05:30
0b86b421c1
Merge pull request #714 from aaronenyeshi/remove-static-hip-device
...
Remove libhip_device.a static library
2018-10-31 14:08:29 +05:30
7f3e7b5334
Merge pull request #713 from scchan/master-hcc_early_finalize_support
...
Support more than one device code blobs in a single .kernel section
2018-10-31 14:04:06 +05:30
f7ba987038
If we've already seen a __global__ function we do not need to re-parse
2018-10-30 23:34:27 +00:00
b270313129
Fixes global symbols tracking in hip_module
2018-10-31 03:22:38 +05:30
bce3de8162
Handle the very confusing dual encoding of the symbol name.
2018-10-30 01:55:09 +00:00
21f044eac8
Fix allocation size of arrays with multiple and/or non-32-bit channels
...
hipMallocArray and hipMalloc3DArray must use sum of bits
of all components.
2018-10-29 18:12:00 +06:00
185fa122ed
Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_get_alignment_and_size_from_metadata
2018-10-28 17:02:10 +00:00
fe1e963299
Rely on code object metadat for kernarg arguments alignof and sizeof.
2018-10-28 17:01:00 +00:00
f5d8842f6a
Add HIP_DUMP_CODE_OBJECT
2018-10-26 14:14:00 -04:00
062398c72f
Adding checks and debug output for fat binary for hip-clang
2018-10-26 14:13:12 -04:00
817b27d530
Remove libhip_device.a static library
...
Move remaining function definitions from device_util.cpp to hip_runtime.h header. We can now remove the static library completely as device_util.cpp was the last file part of target hip::hip_device .
2018-10-25 19:52:35 +00:00
0703a2d0f0
Make HIP functional again with HCC from ROCm 1.9.x
...
Change-Id: I214acdfd0b79dcf783993e44fe31baee64fd4dc3
2018-10-24 10:41:56 +05:30
de5f47a984
Make correct checking of the returned hipDeviceptr_t from read_global_description()
2018-10-23 21:13:11 +08:00
30ce25e627
Support more than one bundles in a single .kernel section
...
When compiling with Early Finalization enabled in HCC,
the resulting .kernel section of the host object now may
contain more than one device code bundles. This is to
teach the HIP runtime to correctly extract all the
bundles from the .kernel section.
2018-10-18 17:00:27 -04:00
Siu Chi Chan
Yaxun Sam Liu
Maneesh Gupta
Qianfeng Zhang
Michael Kuron
Rahul Garg
root
Evgeny
Alex Voicu
Michael Kuron
Anton Gorenko
Aaron Enye Shi