Commit Graph

1377 Commits

Author SHA1 Message Date
Julia Jiang cd7252f82d SWDEV-290704 - Add HIPrtc doxygen in API headers
Change-Id: I629bdeaef7a01aec45bb9453d883213c73008d1c


[ROCm/hip commit: 470f3e521c]
2021-06-10 17:16:01 -04:00
Rahul Garg 4cd9afebe9 SWDEV-288707 - Merge HIP refactored code to staging
These changes move-
- rocclr based implementation inside src/hipamd/src
- platform specific (both nvidia and amd) headers inside
src/hipamd/include/hip

Change-Id: Ia29791a727244952591fe1d813dcef0303b73a9e


[ROCm/hip commit: ce76ec8b88]
2021-06-07 00:07:24 +00:00
German Andryeyev cc3826a126 SWDEV-240804 - Add hipMemAdvise() extension
Add coarse grain memory extension. The new advice will allow HMM
to disable cache coherency policy to improve performance

Change-Id: I3c792d6a96896b983a7ffccddaa0ded06d183212


[ROCm/hip commit: c80955b569]
2021-06-02 16:16:14 -04:00
Joseph Greathouse 9f962f4d74 SWDEV-288361 - Implement funnel shift operators
Change-Id: I0c73809366f2d21e75f98fdeac7fed0c7591ee34


[ROCm/hip commit: bec284b26a]
2021-06-01 11:10:11 -04:00
German Andryeyev a93053443b SWDEV-240804 - Fix typos in the comments
Change-Id: Ic1385daf1e685772b02a11d43fb13f6cde74c4b7


[ROCm/hip commit: b01b048e08]
2021-05-29 00:31:46 -04:00
Aaron En Ye Shi 4eba23b825 SWDEV-283266 - Workaround RTC macro in vector types
Temporarily disable __HIPCC_RTC__ in hip_vector_types.h
while the upstream clang headers are outdated on mainline.
Once upstream patch has landed in mainline, revert this
change. This is a workaround for hiprtc testing.

Change-Id: Ib2cf6023b71431bbfbe3c699076caa4f90f7170c


[ROCm/hip commit: 3899687b8d]
2021-05-21 15:53:59 +00:00
Tao Sang 7a0c6880b6 SWDEV-282588 - Improve clock64()
Let clock64() read s_memtime to prevent rolling over
Add wall_clock64() to read s_memrealtime

Change-Id: I706387355add75852c570be2656131ef99e8968f


[ROCm/hip commit: 7373112d74]
2021-05-17 13:19:04 -04:00
Aaron En Ye Shi 4b9326b6b3 SWDEV-263959 - Fix device decl with long and llong
Windows may expect long and ulong to be 4 bytes, while
Linux expects 8 bytes. Instead, use uint64_t for
unsigned long, and unsigned long long, and use int64_t
for long and long long to be consistent.

Change-Id: I6ed1cdde43721bcaaab0245644d607b1adbf9884


[ROCm/hip commit: 2d6881e26b]
2021-05-14 11:59:27 -04:00
pghafari 8de2b45056 SWDEV-245532 - HIP - Vulkan interop semaphores
Change-Id: I89be5ee84d4728d76e1987d5016c944c0dbc9a96


[ROCm/hip commit: 86a5e82a4b]
2021-05-11 11:44:59 -04:00
Aaron En Ye Shi 8ce60e4a44 SWDEV-283266 - __HIPCC_RTC__ macro added to HIP headers
For hipRTC on Windows, add macro __HIPCC_RTC__ to allow
online compilation of with device functions excluding standard
C/C++ headers, system headers, and host HIP APIs.

Change-Id: I1d91f042baf1359856ec83ab7030dc58785e0334


[ROCm/hip commit: 811bc363c8]
2021-05-10 17:28:07 +00:00
Anusha Godavarthy Surya a76f840701 SWDEV-240806 - Initial commit for hipGraph and stream capture infrastructure
On StreamBegincapture captures the parameters passed to APIs and respective node will be created and added to graph
All parameters are passed to STREAM_CAPTURE macro, it checks if stream in capture mode and redirects the call to the capture function and returns
Updated hipStream and hipEvent with capture parameters
Added handling for hipStreamBeginCapture & hipStreamEndCapture

Change-Id: Ic8926a7b4336c2cc81f0b3a9a224aa392c474134


[ROCm/hip commit: c35ba37287]
2021-05-07 17:38:16 -04:00
Anusha GodavarthySurya f1f38679e5 SWDEV-271978 - Function __byte_perm to match CUDA behavior
Selector indices are as follows (the upper 16-bits of the selector are not used): selector[0] = s<2:0> selector[1] = s<6:4> selector[2] = s<10:8> selector[3] = s<14:12>

Change-Id: Ibf76c6ec2374f1f5b9bba8bd9dbd73660f830eea


[ROCm/hip commit: 1cc65c48a2]
2021-05-05 03:00:32 -04:00
kjayapra-amd 06e4e7ee8f SWDEV-245533 - Implementing Mipmap array APIs
Change-Id: I222c8d0fcbd50cdefd702462e689463bb36366d2


[ROCm/hip commit: 9c07201c6b]
2021-04-30 16:33:43 -04:00
Satyanvesh Dittakavi ae26a2f818 SWDEV-283388 - Fix hipMemRangeGetAttributes on Nvidia Platform
Change-Id: I5daeacd9dd5c6ce7f914d6e6e45dd41fb2a675a5
hipMemRangeGetAttributes was returning hipErrorInvalidValue due to improper
mapping of the arguments to cudaMemRangeGetAttributes.


[ROCm/hip commit: c81a7136d2]
2021-04-29 06:06:03 -04:00
Satyanvesh Dittakavi 14089a9815 SWDEV-281789 - Add missing HMM attributes on CUDA path
Change-Id: I11167eea006301e01a1f91708bf6d0ac832d8b7f


[ROCm/hip commit: fe1268b082]
2021-04-26 13:54:01 -04:00
Yaxun (Sam) Liu cf0ea7f202 SWDEV-255234 - remove workaround for warpSize after clang fix is released
The workaround is no longer needed as the compiler emits the macro itself.

Change-Id: I6a06e73353628bcea71f6bd23503ab6d8e42a29d


[ROCm/hip commit: bf6b451ae3]
2021-04-26 08:49:15 -04:00
Anusha GodavarthySurya 3eb15d6360 SWDEV-282361 - HIP support for NVRTC
Change-Id: I82869af8194b595f9a2fb64ad034630786189335


[ROCm/hip commit: 4de1bfafcc]
2021-04-20 09:28:58 -07:00
Tao Sang abcbcee510 SWDEV-279657 - Fix hipMallocManaged-N256M failure
Add concurrentManagedAccess detection in hipMallocManaged test.
Skip test when device doesn't support concurrentManagedAccess.

Change-Id: Ie54046feef3baba857a7068972ec1fc1a60c2dfd


[ROCm/hip commit: 60e2b1299c]
2021-04-20 09:07:31 -04:00
Sourabh Betigeri 4c043fc89f SWDEV-256723 - Added group partitioning feature in ROCm CG.
Change-Id: Ie54046feef3baba857a7068972ec1fc0a60c2df9


[ROCm/hip commit: 70af64121b]
2021-04-19 18:53:17 -04:00
Julia Jiang 76aa3fbde4 SWDEV-270961 - Update hip_programming_guide.md for event handling
Change-Id: Ieadac9972e5ee13c05ccb42a679866f494f96f47


[ROCm/hip commit: 171551ea8a]
2021-04-16 12:14:25 -04:00
Satyanvesh Dittakavi 94bb45ff6d SWDEV-281504 - Rename structure names to use reserved names in HIP headers
HIP headers use few structure names as X, Y, and Z. This causes
compilation issues when the apps use similar names as macros.
Renamed the struct names to use reserved names such as
__X, __Y and __Z

Change-Id: I59416c3734f274e853c87d4856b7e616f6cee5f5


[ROCm/hip commit: b26ef8522e]
2021-04-15 09:52:58 -04:00
Tao Sang 8e4eab2f4d SWDEV-273138 - Rearrange device attributes
Change-Id: Iab5902c9a2702456fbe437fdefc40541c48abb74


[ROCm/hip commit: ca50ac83c7]
2021-04-12 17:05:27 -04:00
kjayapra-amd f3af2709b4 SWDEV-274276 - Implement system scope atomics to _system builtins. Default atomics will map to agent.
Change-Id: I63b13063274418e96d4be0159c779127b166bea5
(cherry picked from commit 7c4ae8ca1daac0b75ac36c4e4a45b8d13f219d14)


[ROCm/hip commit: dfaf6140cf]
2021-04-09 10:23:32 -04:00
Sarbojit Sarkar 225d149818 SWDEV-260454 - Fix for idenfying bad streams
Change-Id: I122ff6f47535c3c76ab56ba49ab1450ef886b15f


[ROCm/hip commit: 492ccc3281]
2021-04-07 12:13:30 -04:00
Sarbojit Sarkar 47c83726a4 SWDEV-280131 - Fix __half2 member access bug
Change-Id: Ic11750d18e4ba47446a7e494c3089a19cb4df783


[ROCm/hip commit: 83a25eb5b5]
2021-04-07 12:12:02 -04:00
pghafari 5242decbc0 SWDEV-245532 - HIP - Vulkan interop
Change-Id: Iba1ef8112e318b4f099da5a4a4602e0dae7de9e3


[ROCm/hip commit: a1b321bba4]
2021-03-31 10:23:31 -04:00
Sarbojit Sarkar 04849fca63 SWDEV-277926 - Updated deprecated APIs in Cuda
Change-Id: I9ff655af227b245067eb760325c395bb562696ee


[ROCm/hip commit: d4f347747b]
2021-03-29 01:19:19 -04:00
Satyanvesh Dittakavi 70445b1f7e SWDEV-277152 - Add hipMemcpy2DToArrayAsync API in headers
Also, address few scenarios for hipMemcpy2DToArray/Async to return
proper error types

Change-Id: Idbadf666a5e7bebc0f3ea8b7048b79208e04cf6b


[ROCm/hip commit: 39f4d0d244]
2021-03-27 13:50:38 -04:00
jujiang 59acce2b79 SWDEV-277423 - Correct hipStreamWaitValue doxygen format
Change-Id: I8914c14cb7a05d5d0bdfa054af14765c872c70a6


[ROCm/hip commit: d279bd99bb]
2021-03-19 14:10:41 -04:00
Tao Sang f962ea4cc1 SWDEV-273138 - Update canUseStreamWaitValue retrieving
Remove canUseStreamWaitValue from hipDeviceProp_t.
Update canUseStreamWaitValue retrieving in hipDeviceGetAttribute().

Change-Id: I275bd42d8b03e141caaf9f1bc6b714e51ca72dfb


[ROCm/hip commit: ca0cc36ef4]
2021-03-18 22:42:35 -04:00
cjatin 3ecbc923db SWDEV-272811 - Using OCML functions for conversion of fp to int
Change-Id: Id0c02bf6a2e0553d522035b078a9db4cd3fad215


[ROCm/hip commit: 2afa40873a]
2021-03-18 11:43:30 -04:00
Ravi C Akkenapally 276d9ce2cb SWDEV-276827 - Stream Operations: match API with CUDA
Change-Id: Ia79a950561e97df3b2229f76f5512dede2babf98


[ROCm/hip commit: 475d928be8]
2021-03-18 07:52:29 -07:00
Tao Sang 15519dd555 SWDEV-273943 - Enable runtimeApi.event dtest
Add device_id_ in hip::event to match cuda behaviour in
hipEventQuery() and hipEventRecord().
Enable hipEventElapsedTime test on AMD platform.
Workarround sporadic crash of hipEventIpc test due to
some bug of event ipc.
Add missing hipEventDestroy() in some event tests.
Fix some logic code errors.
Fix typo in comment.

Change-Id: I9ec74c475161b3e31df48d193449023e921f2924


[ROCm/hip commit: 38b0c952a6]
2021-03-16 17:12:08 -04:00
jujiang f9b7d37bea SWDEV-270961 - Add doxygen for Texture APIs
Change-Id: I4038320a638292440d9ca8c23ffcabffcd9a48c2


[ROCm/hip commit: 3498f3600a]
2021-03-09 16:23:56 -05:00
Satyanvesh Dittakavi d988defe00 SWDEV-275317 - Fix hipMemcpy2DFromArray to return proper error types
Change-Id: Id722865d81460bfd2fa6ad7a198b6e3c2a08265a


[ROCm/hip commit: 0303084b0e]
2021-03-09 05:22:23 -05:00
Satyanvesh Dittakavi 8b8e7636cd SWDEV-274404 - Add hipDrvMemcpy3D* and hipMemcpy2DFromArray* APIs on HIP CUDA
Change-Id: I4aba2bff60a7bae6b01b6e471968227b0df8e192


[ROCm/hip commit: fba442fe36]
2021-03-08 13:14:25 -05:00
Arya.Rafii 335decd182 SWDEV-269246 - Implementation of hipDrvMemcpy2DUnaligned
Change-Id: I86fdd3b930cbd74c45cd31944f0ea52c0ff65a59


[ROCm/hip commit: 24837c1afc]
2021-03-04 14:38:06 -05:00
Arya.Rafii 20c981abd3 SWDEV-269246 - Added missing exports for hipArrayDestroy
Change-Id: I730814720bb618e895efbe2f412e437110bed8bc


[ROCm/hip commit: 6f1a09b47f]
2021-03-04 14:29:16 -05:00
Ravi C Akkenapally 3d9b4cc2c2 SWDEV-179105 - Stream Operations: Add swqupport for Wait and Write
Change-Id: I9d6d0665d12b62fe705ce1569a0e8264a4f23ab7


[ROCm/hip commit: e89b228eac]
2021-03-02 12:15:46 -08:00
Vladislav Sytchenko a523f75554 SWDEV-232428 - Enable device printf for Windows
Change-Id: Id72cfc34cfcfcbcb459bd8d84979637eaf7947dd


[ROCm/hip commit: 084d25010b]
2021-02-26 11:46:38 -05:00
Satyanvesh Dittakavi 08828176e7 SWDEV-271491 - Fix flags for hipSetDeviceFlags on HIP-CUDA path
Change-Id: I29446d5cc5a26a4b83fa45175ccdf1d8f3a9ea40


[ROCm/hip commit: d134c05699]
2021-02-25 12:06:33 -05:00
Jatin Chaudhary 31983c00f5 SWDEV-272811 - hipCabs returns a double and uses sqrtf, which maps to f32 operation. sqrt should be used instead
Change-Id: I4f74ee8853113fcebfa508bea9308ae93c7ad13b


[ROCm/hip commit: 4d0383df0c]
2021-02-25 08:47:19 -05:00
Jatin Chaudhary 4f4340f4af SWDEV-268531 - Fixing shadow variable warning in vector_types
Change-Id: Ic57e22853529a953582c9194d09133a5aab989aa


[ROCm/hip commit: 22164ebc3f]
2021-02-16 06:51:37 -05:00
Maneesh Gupta e1802c292c SWDEV-271416 - Keep HIP_DYNAMIC_SHARED macro for compat with existing HIP apps
Change-Id: I536e0c65d6e8696cbc369082350834abd710abca


[ROCm/hip commit: debceab2a8]
2021-02-16 00:09:48 -05:00
Maneesh Gupta 800652cef7 SWDEV-269351 - Revert "Implement assert() using the new fprintf_stderr facility"
This reverts commit f0a9c129a0.

Reverting since this is dependent on a device libs change which is not yet in mainline.

Change-Id: I094781b868f39995d1eecb41488c1a1a0147b787


[ROCm/hip commit: 7998429c21]
2021-02-12 03:46:17 -05:00
cjatin cb46badf20 SWDEV-268531 - Fixing shadow varible warning seen with hip vector usage
Change-Id: I9e20a41e74e473b328cc173f2c27b06352128c88


[ROCm/hip commit: a12163b4e5]
2021-02-09 13:33:12 -05:00
Julia Jiang ef396373ec SWDEV-271416 - Remove HIP_DYNAMIC_SHARED macro in hip
Change-Id: I12f39ea8438eb7ce76d8ffb2151b4faa93689048


[ROCm/hip commit: 090b2829b9]
2021-02-08 13:17:46 -05:00
Sarbojit Sarkar 3fa56865cc SWDEV-265469 - added constexpr constructor for dim3
Change-Id: I2e23a403f272d1ff0ade24fec11190d2f3244e5f


[ROCm/hip commit: 09b1eb8c9f]
2021-01-28 13:23:51 -05:00
Satyanvesh Dittakavi 89fec911e8 SWDEV-269784 - managed memory support for HIP CUDA
Change-Id: I01f9fc64573f402031eceab24395e5cbd93007f9


[ROCm/hip commit: 25cccbb60d]
2021-01-28 07:51:52 -05:00
Tao Sang 8679ca98aa SWDEV-268757 - Disable deprecation warning
Disable it as it will fail rocgdb test

Change-Id: Ibf34c780d5bd4278adcedba1d6e057639c258483


[ROCm/hip commit: 30820b131e]
2021-01-21 15:35:32 -05:00