Commit grafiek

902 Commits

Auteur SHA1 Bericht Datum
Maneesh Gupta 09fe2d6bc5 Map more instrincis to ocml native
Change-Id: I54e55d5902931bafdabd0956e4e8c1d7b39f7173


[ROCm/hip commit: dd9bea7d25]
2019-01-15 19:40:37 +05:30
Maneesh Gupta 5db57f36d7 Switch to faster ocml variants for trig instrinsics
Change-Id: If62821e2fe1b0da91ad1b8c5580ebf1a009405e9


[ROCm/hip commit: 2b9d52b210]
2019-01-14 13:01:57 +05:30
Laurent Morichetti 0597dc63df Fix compilation issues with MSVC
[ROCm/hip commit: c9f552968d]
2019-01-09 09:32:50 -08:00
Alex Voicu 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
Alex Voicu 7bcb83a05f Start re-working 731 for 2.0.
[ROCm/hip commit: 25c7e5d609]
2019-01-01 11:00:57 +05:30
Maneesh Gupta 09a02a63a7 Merge pull request #818 from yxsamliu/fix-hip-config
Add default arguments for hipConfigureCall

[ROCm/hip commit: 4d0266a495]
2019-01-01 10:25:25 +05:30
Yaxun Sam Liu a2ab2b0370 Use __dparm for default parameter
[ROCm/hip commit: 548f4dd4e5]
2018-12-31 13:07:19 -05:00
Yaxun Sam Liu e9532108bb Add default arguments for hipConfigureCall
[ROCm/hip commit: ec03a8b352]
2018-12-18 15:48:21 -05:00
Aaron Enye Shi 8e7b49d1cf Add *_rn functions back into HIP intrinsics
Add back the round-to-nearest-even intrinsics back to HIP math
intrinsics as it caused regression.


[ROCm/hip commit: 58dfeff27a]
2018-12-18 19:31:54 +00:00
Siu Chi Chan bca8022aa0 Revert "Rely on code object metadat for kernarg arguments alignof and sizeof."
This reverts commit 6d64f5e112.


[ROCm/hip commit: 1fbf639962]
2018-11-29 11:38:37 -05:00
Siu Chi Chan f04655ff6e Revert "Handle (odd) corner case of argumentless __global__ function."
This reverts commit 591d4d1b5f.


[ROCm/hip commit: aeca2c8cdc]
2018-11-29 11:38:34 -05:00
Maneesh Gupta 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
Michael Kuron c35dfb71d5 Merge branch 'master' into getsymboladdress
[ROCm/hip commit: 8610128c3e]
2018-11-20 12:03:22 +01:00
Michael Kuron 2e8a94e90b Fix hipGetSymbolAddress/hipGetSymbolSize on nvcc
[ROCm/hip commit: 999b62b711]
2018-11-15 09:48:00 +01:00
Maneesh Gupta bc85e694c5 Merge pull request #756 from yxsamliu/fix-heap
Define __hip_device_heap in header for hip-clang only

[ROCm/hip commit: 0770c2b8da]
2018-11-14 13:22:31 +05:30
root dbc30b7800 rebase to master, tracer related changes
[ROCm/hip commit: 091124a766]
2018-11-13 15:50:34 +00:00
Evgeny 74488844fb specialized spawner object
[ROCm/hip commit: 32c0008ef6]
2018-11-13 15:33:26 +00:00
Evgeny 73e3c4ec42 renaming HIP_INIT_CB_API to HIP_INIT_API
[ROCm/hip commit: e5ba097afd]
2018-11-13 15:33:26 +00:00
Evgeny 7f6832cbe5 hip_prof_(api/str).h moving under hcc_detail dir
[ROCm/hip commit: 47f1d059d1]
2018-11-13 15:33:26 +00:00
Evgeny db784eff1d compilation fix - struct name fix
[ROCm/hip commit: 5d6a6a5c6c]
2018-11-13 15:33:26 +00:00
Evgeny 0349de4f51 fix
[ROCm/hip commit: ec989ffd96]
2018-11-13 15:33:26 +00:00
Evgeny 0a58dc9b7b adding activity prof layer
[ROCm/hip commit: b8b1637ef7]
2018-11-13 15:33:26 +00:00
Yaxun Sam Liu a30829a7bf Define __hip_device_heap in header for hip-clang only
[ROCm/hip commit: 17ac81b69e]
2018-11-12 16:39:41 -05:00
Alex Voicu 591d4d1b5f Handle (odd) corner case of argumentless __global__ function.
[ROCm/hip commit: c0bd1a5af8]
2018-11-12 00:32:35 +00:00
Alex Voicu 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
Aaron Enye Shi 8bf2429663 Guard rcp rounded implementation as well
Since rcp implementations of non-default rounded versions are not correct or supported in OCML, guard them using the same macro OCML_BASIC_ROUNDED_OPERATIONS. Also update the docs and tests.


[ROCm/hip commit: 0cfaa52d15]
2018-11-06 19:53:28 +00:00
Aaron Enye Shi eb4053e3fe Guard the OCML rounded operations instead
Instead of commenting all these functions out, guard the functions with a macro OCML_BASIC_ROUNDED_OPERATIONS.


[ROCm/hip commit: e59c33250a]
2018-11-06 16:32:14 +00:00
Michael Kuron cbba8221ee Introduce ihipModuleGetGlobal
[ROCm/hip commit: 31acf1c268]
2018-11-06 09:54:34 +01:00
Aaron Enye Shi 1c6f47ef55 Remove non-working non-default-rounded math apis
In ROCm-Device-Libs, they have dropped the non-default-rounded versions of add, sub, mul, div, sqrt and fma. Therefore, ocml has removed the rte, rtp, rtn, and rtz counterparts. This will remove the same math APIs in HIP for _ru, _rd, _rn, and _rz.


[ROCm/hip commit: 2b108a2cfd]
2018-11-05 22:34:16 +00:00
Michael Kuron da5df1fd1e Document return values of hipMemcpyToSymbol, hipGetSymbolAddress
[ROCm/hip commit: 4390c82121]
2018-11-04 11:47:17 +01:00
Michael Kuron bc455ccf50 Implement hipGetSymbolAddress and hipGetSymbolSize
[ROCm/hip commit: 73616582d6]
2018-11-04 10:39:34 +01:00
Alex Voicu 9cd4a9dbb1 Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_get_alignment_and_size_from_metadata
[ROCm/hip commit: f28cde3f98]
2018-11-01 23:17:27 +00:00
Siu Chi Chan 1159b4aa05 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


[ROCm/hip commit: 0ff408a56c]
2018-11-01 16:20:35 -04:00
Jeff Daily c28043bc4f typedef struct hipFuncAttributes now C compatible.
Fixes #591.
Fixes #694.


[ROCm/hip commit: bb447dd76e]
2018-10-31 14:12:45 +05:30
Maneesh Gupta ac071f5390 Merge pull request #714 from aaronenyeshi/remove-static-hip-device
Remove libhip_device.a static library

[ROCm/hip commit: 0b86b421c1]
2018-10-31 14:08:29 +05:30
Maneesh Gupta 3986e47f8d Merge pull request #713 from scchan/master-hcc_early_finalize_support
Support more than one device code blobs in a single .kernel section

[ROCm/hip commit: 7f3e7b5334]
2018-10-31 14:04:06 +05:30
Alex Voicu 726b654c6d Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_get_alignment_and_size_from_metadata
[ROCm/hip commit: d035cb9000]
2018-10-30 23:34:46 +00:00
Alex Voicu c998b7dfc2 Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into feature_get_alignment_and_size_from_metadata
[ROCm/hip commit: 185fa122ed]
2018-10-28 17:02:10 +00:00
Alex Voicu 6d64f5e112 Rely on code object metadat for kernarg arguments alignof and sizeof.
[ROCm/hip commit: fe1e963299]
2018-10-28 17:01:00 +00:00
Aaron Enye Shi 5bbd632888 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 .


[ROCm/hip commit: 817b27d530]
2018-10-25 19:52:35 +00:00
Alex Voicu 147a6bab43 hipLaunchKernel, hipLaunchParm are deprecated, and shall be removed.
[ROCm/hip commit: e4181b85be]
2018-10-25 13:32:17 +01:00
Maneesh Gupta 5333a22ccc Merge pull request #723 from mangupta/fix_double_shfl
Fix logic for double variants of __shfl*

[ROCm/hip commit: f6f160fa6b]
2018-10-25 06:01:38 +05:30
Maneesh Gupta dd8ebc9a97 Fix logic for double variants of __shfl*
Change-Id: I604f00b54cf4bd9c5f26ca6fa680fca5e9629417


[ROCm/hip commit: 19404e603d]
2018-10-24 12:39:09 +05:30
Maneesh Gupta 90d15c13a1 Make HIP functional again with HCC from ROCm 1.9.x
Change-Id: I214acdfd0b79dcf783993e44fe31baee64fd4dc3


[ROCm/hip commit: 0703a2d0f0]
2018-10-24 10:41:56 +05:30
Maneesh Gupta a648f1c48e Merge pull request #705 from ROCm-Developer-Tools/feature_minimal_changes_for_hc_next
Feature minimal changes for hc next

[ROCm/hip commit: 4a00b244a3]
2018-10-19 06:58:31 +05:30
Siu Chi Chan 7ce37f3a08 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.


[ROCm/hip commit: 30ce25e627]
2018-10-18 17:00:27 -04:00
Alex Voicu b8b15ce792 Dumb workaround is still needed, so add it back.
[ROCm/hip commit: 5ccaf2fa7d]
2018-10-18 15:33:46 +01:00
Alex Voicu de15c6988d Re-sync with upstream.
[ROCm/hip commit: fe959f7bd7]
2018-10-18 12:27:03 +01:00
Maneesh Gupta 0dff12a615 Merge pull request #688 from aaronenyeshi/fix-sinf-cosf-ocml
Use sinf and cosf from ocml device libs

[ROCm/hip commit: 1a5025c57e]
2018-10-18 16:39:20 +05:30
Maneesh Gupta 1a8b4ce037 Merge pull request #692 from whchung/hip-reinit-take2
HIP program state re-initialization logic (take 2)

[ROCm/hip commit: d133493669]
2018-10-18 12:06:41 +05:30