Commit Graph

12807 Commits

Author SHA1 Message Date
Chauncey Hui 2b133ed3de SWDEV-2 - Change OpenCL version number from 3289 to 3290 2021-04-10 03:00:06 -04:00
Jason Tang 1a38be8972 SWDEV-277559 - Remove AMDIL
The rest of AMDIL support will be removed along with orca backend.

Change-Id: I0462501e7147dc4b99870fd02034d0a4a0496e55
2021-04-09 14:15:15 -04:00
Saleel Kudchadker 9307ab43e4 SWDEV-278336 - Print time info only when profiling
Change-Id: Ic8d04e58cf4558fbfc5ed6db35f3ff2d788803f9
2021-04-09 13:17:31 -04:00
kjayapra-amd 61d1eaa522 SWDEV-274276 - Implement system scope atomics to _system builtins. Default atomics will map to agent.
Change-Id: I63b13063274418e96d4be0159c779127b166bea5
(cherry picked from commit 7c4ae8ca1daac0b75ac36c4e4a45b8d13f219d14)
2021-04-09 10:23:32 -04:00
Chauncey Hui bb9c9c4322 SWDEV-2 - Change OpenCL version number from 3288 to 3289 2021-04-09 03:00:06 -04:00
Satyanvesh Dittakavi 191ce1dd05 SWDEV-279486 - Fix hipMemcpyPeer/hipMemcpy APIs
Addresses the scenarios when the size passed is more than
the allocated size and when the deviceid is invalid
Change-Id: I6c9b62639096f655ffb61976905b1ce8c5f51ee7

Change-Id: I8a0d660924a8e2300c517aba6f9088626b8f6ef5
2021-04-09 02:53:15 -04:00
Julia Jiang ea0e2007c0 SWDEV-270961 - Update HIP FAQ.md
Change-Id: I34b03692edd9e6bc424a3ee615d21cb226aa86cf
2021-04-08 14:13:13 -04:00
Konstantin Zhuravlyov 3010cf0a58 SWDEV-76911 - Target ID workarounds in vdi runtime:
- Add HSAIL ID for Hawaii as gfx702
  - Add HSAIL ID for Renoir without xnack as gfx90c

Fixes: SWDEV-271289, SWDEV-272761
Change-Id: I92cf4619cdfd550462ff8ec3740443ef1e5a5f96
2021-04-08 12:14:25 -04:00
Chauncey Hui 96e67ce3e5 SWDEV-2 - Change OpenCL version number from 3287 to 3288 2021-04-08 03:00:06 -04:00
Saleel Kudchadker aa38af8c96 SWDEV-276120 - Remove support for barrier sync
ROC_BARRIER_SYNC will not work with direct dispatch.
Remove and cleanup.

Change-Id: I81368b2e65039477bd0343bb92708dab48867db6
2021-04-07 17:08:39 -04:00
Sourabh Betigeri 48e470a14c SWDEV-273265 - Reverting wrong scope resolution operator VirtualGpu in the declaration releaseGpuMemoryFence()
Change-Id: Ia67ee1e4a3e86235caf8b7c585c65372f7d55426
2021-04-07 09:24:10 -07:00
Sarbojit Sarkar daf0cbca3c SWDEV-260454 - Fix for idenfying bad streams
Change-Id: I122ff6f47535c3c76ab56ba49ab1450ef886b15f
2021-04-07 12:13:30 -04:00
Sarbojit Sarkar 9cbb283771 SWDEV-280131 - Fix __half2 member access bug
Change-Id: Ic11750d18e4ba47446a7e494c3089a19cb4df783
2021-04-07 12:12:02 -04:00
Chauncey Hui a22df8f7f3 SWDEV-2 - Change OpenCL version number from 3286 to 3287 2021-04-07 03:00:06 -04:00
Rupam Chetia c9ef2adf6a SWDEV-238517 - [dtest] Adding additional scenarios for block and grid dimension.
1. Corner case and negative test scenarios added for block and grid dimension.

Change-Id: I094faf02570fec101f688462712934b94ceb37e1
2021-04-07 01:44:39 -04:00
Sarbojit Sarkar d8d6c4e55d SWDEV-280089 - nullptr was getting added into MemObj
Change-Id: Ica56126156198140a143182de3d93d86730cadf1
2021-04-06 23:41:50 -04:00
Sourabh Betigeri 21ea81d5b9 SWDEV-273265 - Fix to wait on a pending dispatch in PAL.
Change-Id: I431cedfef5d5cb727c35ba8e294528017bfe2088
2021-04-06 13:13:07 -04:00
Julia Jiang f22ceb0fd8 SWDEV-272268, SWDEV-268186 - OCL change for Rebar optimization:fix regressions in OCLMemInfo and Conformance basic test
Change-Id: I3e709942b5f43ba52a4cb0824a2e6b3202d4b405
2021-04-06 10:53:12 -04:00
German Andryeyev 2d41031aec SWDEV-279288 - Move the batch condition
The check has to be performed inside the signal loop, because
active signals need to be processed to avoid a stale timestamp
class.

Change-Id: I26af8287aae18eb19c096d9358cd0b86cfd1c561
2021-04-06 10:22:31 -04:00
Rupam Chetia bbc933c914 SWDEV-238517 - [dtest] Adding new test cases for hipComplex functions.
1. Added 21 test scenarios to test the hipComplex functions on both host and device.
2. Modified the floating point comparisons with precision check.

Change-Id: I9edfb0c635ced255935087c85b77d3cc6a1a82e3
2021-04-06 07:54:29 -04:00
Chauncey Hui e919404eab SWDEV-2 - Change OpenCL version number from 3285 to 3286 2021-04-06 03:00:07 -04:00
Julia Jiang 774565e5ae SWDEV-270961 - update HIP documents
Change-Id: I5168d83a124e9c7d856fb7a46d9960d9f99143c6
2021-04-05 14:34:33 -04:00
German Andryeyev a71f7f931e SWDEV-279288 - Avoid profiling info for the sync barrier
- With direct disaptch profiling state is enabled to trigger the
callback on HSA signal. However ROCr has very low peformance on
the first call to get the profiling info. That impacts some tiny
performance tests.

Change-Id: Idacd1b10a473fcfb5feef3074b7191d35743f769
2021-04-05 12:54:23 -04:00
Satyanvesh Dittakavi 380d903402 SWDEV-277264 - Support install.sh on CentOS
Change-Id: I2e83c53f68372c4de538cc67414440a933241814
2021-04-05 09:06:05 -04:00
Chauncey Hui 811f78f7d1 SWDEV-2 - Change OpenCL version number from 3284 to 3285 2021-04-02 03:00:06 -04:00
Todd tiantuo Li 0d7ded0bfb SWDEV-1 - enable gfx90c for ROC and PAL paths
Change-Id: If5c4f1ca1b136e14b9e11cd27b1beff386adc377
2021-04-01 12:02:08 -07:00
Sarbojit Sarkar 4af7a74482 SWDEV-276319 - Added null checks
Change-Id: Ib22a333f0f599c8f0efca34f2a287bc4b118d743
2021-04-01 05:11:16 -04:00
Chauncey Hui 47ff27e0db SWDEV-2 - Change OpenCL version number from 3283 to 3284 2021-04-01 03:00:07 -04:00
Sarbojit Sarkar 35c8493237 SWDEV-254441 - Fixed review comments
Change-Id: Ica13f23638be04216d152821127b2b7316f96af0
2021-04-01 00:21:19 -04:00
Alex Xie 0de4b2962c SWDEV-268914 - Linux, AMF, tests fail to scale images down
This is part 2 of the change. This is for PAL backend.
The parent buffer sometimes has newer data than the sub buffer or image.
We always need to copy the data into copybuffer in pitch workaround.

Tests:
clinfo
Conformance tests: all images test, info, API, basic.
Internal runtime tests

Change-Id: I97d876ac75b240e69b48244be4c9e522db24f8ac
2021-03-31 11:17:56 -04:00
pghafari a9304f6111 SWDEV-245532 - HIP - Vulkan interop
Change-Id: Iba1ef8112e318b4f099da5a4a4602e0dae7de9e3
2021-03-31 10:23:31 -04:00
Anusha GodavarthySurya d9debabdc3 SWDEV-278873 - hipStreamCreate handle invalid flag value
Change-Id: I05c0e0b76f7b09947e48d5b9f225af305bade27f
2021-03-31 07:59:41 -04:00
Chauncey Hui 925da60e88 SWDEV-2 - Change OpenCL version number from 3282 to 3283 2021-03-31 03:00:06 -04:00
Jatin Chaudhary 32498b61ff SWDEV-279372 - HIP_CLANG_PATH should resolve from HIP_PATH if its defined
Change-Id: Iee909f1e2f3d6443b494846219ad955a1f0ebfe8
2021-03-31 00:31:45 -04:00
Alex Xie 090cf6c6d3 SWDEV-276304 - [Navi][OpenCL][Linux]AMF Converter generate corrupted Frames
This is part 2 of the code change for PAL.
The copy image workaround could be recursively used by ROCclr blit kernel.
Avoid such situation by using stack variable.

Tests:
clinfo.
Conformance tests - basic, API, info, and all images tests.
Internal runtime tests - all passed.

Change-Id: I3c822e55398cdf35c2c4a46ed9fc20fbee7cc908
2021-03-30 15:56:01 -04:00
Sourabh Betigeri 2ba421f784 SWDEV-274727 - Disabling tests temporarily
Change-Id: I695daebe15f592afdfee8e4efe4d8966b6e9922a
2021-03-30 13:02:19 -04:00
Alex Xie 2bd1836049 SWDEV-276304 - [Navi][OpenCL][Linux]AMF Converter generate corrupted Frames
The copy image workaround could be recursively used by ROCclr blit kernel.
Avoid such situation by using stack variable.

Change-Id: Iadaa8cad9216220194760dd461a9533bb236aea0
2021-03-30 12:07:00 -04:00
sumanthtg 5a84691e52 SWDEV-278478 - hipDeviceGetPCIBusId-vs-lspci test enabled only for linux environment
Change-Id: Ia86174505d912a32b07e8e959adfba6391c3284d
2021-03-30 09:28:28 -04:00
Chauncey Hui 654f51dfc8 SWDEV-2 - Change OpenCL version number from 3281 to 3282 2021-03-30 03:00:08 -04:00
Jatin Chaudhary 8e9e8f40e4 SWDEV-278810 - Remove default addition of CXX Flags if file type is not recognized
Change-Id: I2b29f246d138b511d77f8e78f273795b4977313f
2021-03-30 00:47:56 -04:00
pghafari f1d58ae0d6 SWDEV-245532 - HIP - Vulkan interop
Change-Id: I741f48e095c203bb1304f5b5e44f8c87b14b5497
2021-03-29 12:06:35 -04:00
Sarbojit Sarkar b7a03695c3 SWDEV-277926 - Updated deprecated APIs in Cuda
Change-Id: I9ff655af227b245067eb760325c395bb562696ee
2021-03-29 01:19:19 -04:00
Satyanvesh Dittakavi 68abfb4aff SWDEV-277152 - Add hipMemcpy2DToArrayAsync API in headers
Also, address few scenarios for hipMemcpy2DToArray/Async to return
proper error types

Change-Id: Idbadf666a5e7bebc0f3ea8b7048b79208e04cf6b
2021-03-27 13:50:38 -04:00
Chauncey Hui 682c87592c SWDEV-2 - Change OpenCL version number from 3280 to 3281 2021-03-27 03:00:07 -04:00
pghafari e64ce02ea2 SWDEV-245532 - HIP - Vulkan interop
Change-Id: I0be4279bb1037640d138dd07e125b78a719743ca
2021-03-26 13:59:13 -04:00
Chauncey Hui 69eccabbc5 SWDEV-2 - Change OpenCL version number from 3279 to 3280 2021-03-26 03:00:05 -04:00
pghafari 74de707cf2 SWDEV-245532 - HIP - Vulkan interop, syntax update
Change-Id: I5fd4431bab4d975efec47298f2746fbcbbec8a44
2021-03-25 13:40:55 -04:00
German Andryeyev 8c513407af SWDEV-278346 - Replace assert with LogWarning()
ROCr returns some unexpected values and for now just return
invalid device back to the app

Change-Id: Ia6fb709ed2dc77d77bd5d64de80b41b3720bed76
2021-03-25 10:19:33 -04:00
Chauncey Hui 226af92939 SWDEV-2 - Change OpenCL version number from 3278 to 3279 2021-03-25 03:00:07 -04:00
Maneesh Gupta dff604f557 SWDEV-187253 - Print warning if launch_params > bounds
Change-Id: I138546bf816887576e797105f97ce37245911045
2021-03-24 22:29:19 -07:00