AI/rocm-systems
2
0
Garpu 0
Kode Masalah Tarik Permintaan Actions Packages Projects Rilis Wiki Kegiatan
4.219 Melakukan 3 Cabang 0 Tag
788ae8595b00879decd4cc5cfa436b4e475317bc
Grafik Komit

4219 Melakukan

This Branch
This Branch
All Branches
Penulis SHA1 Pesan Tanggal
kjayapra-amd 788ae8595b SWDEV-295144 - Change uint64_t to size_t to fix failure on 32-bit opencl. 
Change-Id: I5c28e9c606dec1c956f3f48071d8a0271adfff22
 2021-08-22 23:56:08 -07:00
Chauncey Hui 650601c00e SWDEV-2 - Change OpenCL version number from 3344 to 3345 2021-08-22 23:56:08 -07:00
anusha GodavarthySurya 682151f39d SWDEV-295251 - Avoid marker if queue is empty for DD to fix MT issue 
Change-Id: I80be39ace9d93347f81ef8acd7858d43bc4a3f1e
 2021-08-22 23:56:08 -07:00
Vladislav Sytchenko de53cd1903 SWDEV-240806 - Fix Windows build 
Fixes error "All control paths should return a value".

Change-Id: I4718688b55b24862465e15ea0d64b32fa44b3299
 2021-08-22 23:56:08 -07:00
Vladislav Sytchenko ffbf368f4c SWDEV-293519 - [PAL] Limit mgpu SVM logic only to mgpu cases 
Below logic allocates the host buffer whenever a subbuffer is created
from a SVM allocation. This is only needed for multi-device contexts.

HIP does not support multi-device contexts, hence this logic just ends
up performing unnecessary system allocations.

Change-Id: I8eae635f7c5289c52ef73434218c1658b788a456
 2021-08-22 23:56:08 -07:00
Chauncey Hui 255f27fd7a SWDEV-2 - Change OpenCL version number from 3343 to 3344 2021-08-22 23:56:08 -07:00
anusha GodavarthySurya 050d54b503 SWDEV-240806 - Add methods to update kernel command parameters 
Change-Id: Iba90a31f9c5d6d4f2b60b7ccf903325c03d4d245
 2021-08-22 23:56:08 -07:00
anusha GodavarthySurya de5168fdef SWDEV-295251 - Remove waitEvent check in append 
Change-Id: I994f3e7c67ed29c4ee46229c8bcd1448fc7f59ec
 2021-08-22 23:56:08 -07:00
Chauncey Hui 3d4fb78a45 SWDEV-2 - Change OpenCL version number from 3342 to 3343 2021-08-22 23:56:08 -07:00
Aaron Liu c6574cb906 SWDEV-294027 - [Lnx][YC] Add Yellow Carp support 
Only add Roc path and don't use Pal path.

Signed-off-by: Aaron Liu <aaron.liu@amd.com>
Change-Id: I7117e2dc3c3ad4c8d563e9bbdc721f70ddba51fd
 2021-08-22 23:56:08 -07:00
Chauncey Hui 76a3a42d38 SWDEV-2 - Change OpenCL version number from 3341 to 3342 2021-08-22 23:56:08 -07:00
Satyanvesh Dittakavi 924695fb5e SWDEV-292021 - Fix Device Reset 
- Device Reset should not purge the allocations that were not by the user
- Addresses QMCPack Test abort due to the removal of all the mem objects during reset

Change-Id: I7b7a123e72bcc985d7e51d17c2382bc618d3e041
 2021-08-22 23:56:08 -07:00
Sourabh Betigeri 8c5c2befeb SWDEV-292523 - [vdi]Change in the signature of streamOperations APIs, particularly 'value' arg to unsigned 'value 
Change-Id: I74b24b2dec911acd5e7a364ea8c050c2ecb1c3b8
 2021-08-22 23:56:08 -07:00
Chauncey Hui f608292e27 SWDEV-2 - Change OpenCL version number from 3340 to 3341 2021-08-22 23:56:08 -07:00
Vladislav Sytchenko 6566361144 SWDEV-283981 - Revert "SWDEV-283981 - [PAL] Support hostcall SQ interrupt" 
This reverts commit 9df70fa03ce60d47247eb0e8f278e1f8dbd33d6e.

Reason for revert: need SWDEV-294782 to be resolved before we can enable SQ interrupt support.

Change-Id: I328170b60f1a3aab28c0b1fd3191297a1a51ecb7
 2021-08-22 23:56:08 -07:00
Chauncey Hui a733679b40 SWDEV-2 - Change OpenCL version number from 3339 to 3340 2021-08-22 23:56:08 -07:00
Vladislav Sytchenko 0a59c9c4c3 SWDEV-291787 - Fix Windows build 
Change-Id: I1b97a1100e4c498f53aaad7157f21d0c5f8a130d
 2021-08-22 23:56:08 -07:00
jujiang 84b971c7c1 SWDEV-291787 - Fix persistent direct map 
Change-Id: Ic1507cc6d63e9ed574e8e169bce7bf56f4792c19
 2021-08-22 23:56:08 -07:00
German Andryeyev 2babcfbdbb SWDEV-290384 - Enable active wait on CPU if HIP requested 
Change-Id: Idea5adf7a4705cb999da6785e6229fe3200dce17
 2021-08-22 23:56:08 -07:00
Vladislav Sytchenko 4589343c3e SWDEV-283981 - [PAL] Support hostcall SQ interrupt 
Change-Id: Ic6f0ad384404712d5eeb1eaf600e231a8f8631f7
 2021-08-22 23:56:08 -07:00
Vladislav Sytchenko 74ccf71d53 SWDEV-294514 - Limit HIP-GL interop logic to HIP 
Below logic is causing a crash in the CL-GL interop. As a workaround,
limit it only to HIP.

Change-Id: I12e81d035ebd80a4a9a09eb6eea2fae7040d90c9
 2021-08-22 23:56:08 -07:00
German Andryeyev c144383971 SWDEV-290384 - Disable HSA callback for any host wait 
Change-Id: Ie876deb62859f5551f4ed69eb8187ac3fa35f42a
 2021-08-22 23:56:08 -07:00
Chauncey Hui 137954b238 SWDEV-2 - Change OpenCL version number from 3338 to 3339 2021-08-22 23:56:08 -07:00
German Andryeyev ff15c0893e SWDEV-292018 - Switch to internal signals for markers 
Add ref counting to ProfilingSignal class to track the last release.
If a signal was used in the marker, then don't reuse it,
but create a new one for internal usage.
Don't rely on HSA callback for the command status update if there
are no pending dispatches.

Change-Id: I19f14ed9d80acfe79993b343b2187635f8428a20
 2021-08-22 23:56:07 -07:00
Sourabh Betigeri 6408b9b906 SWDEV-290685 - Relacing release fence instead of acquire for hipStreamWrite() 
Change-Id: Ic2946b68c427d3e058948c0813863a27c21b903d
 2021-08-22 23:56:07 -07:00
Vladislav Sytchenko a2612343d5 SWDEV-273235 - [PAL] Ignore system headers on Linux 
CMake always searches system paths for specified files before resorting
to the hints we give it. We should not be using elf and GL headers
from /usr/include.

Change-Id: I2172ce3da9cc101ced63e22d95ecc031b94f0a67
 2021-08-22 23:56:07 -07:00
Chauncey Hui db104d71c8 SWDEV-2 - Change OpenCL version number from 3337 to 3338 2021-08-22 23:56:07 -07:00
kjayapra-amd e01a24d8b5 SWDEV-295144 - Typecast arena mem ptr(0x2) to void*, otherwise results in wrong constructor overload. 
Change-Id: I433b70dc70377ae0c5f9b29818703e1ac9d95053
 2021-08-22 23:56:07 -07:00
German Andryeyev e4dae85ade SWDEV-290495 - Add HSA_AMD_AGENT_INFO_SVM_DIRECT_HOST_ACCESS query 
Change-Id: Ib18a53a9016eb5c5ffd51bf6835cba7299ec8421
 2021-08-22 23:56:07 -07:00
Chauncey Hui 7535199f78 SWDEV-2 - Change OpenCL version number from 3336 to 3337 2021-08-22 23:56:07 -07:00
Sourabh Betigeri e4ddb5e08a SWDEV-290685 - Dispatch a barrier packet with acquire system scope to ensure ordering before a hipStreamWrite() 
Change-Id: I8853ad86a6634d55a98173ca3f79d93b85c08f85
 2021-08-22 23:56:07 -07:00
Chauncey Hui 66ccdf6fb5 SWDEV-2 - Change OpenCL version number from 3335 to 3336 2021-08-22 23:56:07 -07:00
Vladislav Sytchenko 6ff4839d76 SWDEV-273235 - Remove dependency on ADL 
Currently ADL is only being included if we build HSAIL and not LC. The
only configuration that does this is Ellesmere on Linux.

As the appprofile logic doesn't do anything right now, it should be
safe to remove it.

Change-Id: I13ce8c27af08c25b95edcbfd2ee1ce447b0bfd39
 2021-08-22 23:56:07 -07:00
German Andryeyev f34c1b9ff8 SWDEV-292820 - Add a new notify lock 
HSA signal calback may occur during the actual marker submit. That
may cause a deadlock, because shared lock_ object. Create the new
notify_lock_ field to protect the notification.

Change-Id: I9752af84e59895530620fac3932c6fc276de8658
 2021-08-22 23:56:07 -07:00
Chauncey Hui 56d9240da4 SWDEV-2 - Change OpenCL version number from 3334 to 3335 2021-08-22 23:56:07 -07:00
Vladislav Sytchenko 970bc2c4f5 SWDEV-273235 - Restore missing LinuxPro option 
Change-Id: Iccc0206f3f2c5b3c03f6ed313537f0f364a4ca29
 2021-08-22 23:56:07 -07:00
Chauncey Hui ed7675ce51 SWDEV-2 - Change OpenCL version number from 3333 to 3334 2021-08-22 23:56:07 -07:00
agunashe d96481fb36 SWDEV-293742 - Update copyright end year VDI repo 
Change-Id: I69d2fea4a7a43adf96ccea794270e4af991c5261
 2021-08-22 23:56:07 -07:00
Chauncey Hui b065eb2d00 SWDEV-2 - Change OpenCL version number from 3332 to 3333 2021-08-22 23:56:07 -07:00
Saleel Kudchadker cd21af757e SWDEV-260448 - Honor NUMACTL for Direct Dispatch 
Setting AMD_CPU_AFFINITY=1 will keep Async Handler thread within the
bounds set by numactl.

Change-Id: Id01b30df5127d65c29ac072bf74a04986b7128de
 2021-08-22 23:56:07 -07:00
German Andryeyev f4032401cf SWDEV-289378 - Avoid CPU TS overwrite if GPU TS is available 
Change-Id: I444ec284669b6a6fff31182e213b47c562c90192
 2021-08-22 23:56:07 -07:00
German Andryeyev 4fd506cfe1 SWDEV-289378 - Avoid CPU TS overwrite if GPU TS is available 
Change-Id: I2fc1a43c048b4fa1e42f27c4cf5c72fc7ae84e9c
 2021-08-22 23:56:07 -07:00
Chauncey Hui 50a50c66b9 SWDEV-2 - Change OpenCL version number from 3331 to 3332 2021-08-22 23:56:07 -07:00
jujiang ed0e7f659d SWDEV-286322 - Add .gitattribute 
Change-Id: I4ae4c4498765f10c98bb5f2443a083463b0e25af
 2021-08-22 23:56:07 -07:00
Chauncey Hui 1d9bf4f0b9 SWDEV-2 - Change OpenCL version number from 3330 to 3331 2021-08-22 23:56:07 -07:00
pvellien c11c02f2c7 SWDEV-285333 - Introduce Address sanitizer hostcall service 
Change-Id: Id29aacd09d0a9934a027446c57c7095804e1a454
 2021-08-22 23:56:07 -07:00
Chauncey Hui ffa29fad01 SWDEV-2 - Change OpenCL version number from 3329 to 3330 2021-08-22 23:56:07 -07:00
German Andryeyev 6ab8dcc682 SWDEV-292018 - Avoid marker if queue is empty 
Change-Id: I40a42d67d2c911d2c9a0bf425f36bc795f9539c0
 2021-08-22 23:56:07 -07:00
Vladislav Sytchenko f6c00765e7 SWDEV-274815 - [PAL] Navi24 support 
Change-Id: I934797bda471618c3f69484a1552b37345ae638b
 2021-08-22 23:56:07 -07:00
Chauncey Hui a58ef5dd8f SWDEV-2 - Change OpenCL version number from 3328 to 3329 2021-08-22 23:56:07 -07:00