e4dae85ade
SWDEV-290495 - Add HSA_AMD_AGENT_INFO_SVM_DIRECT_HOST_ACCESS query
...
Change-Id: Ib18a53a9016eb5c5ffd51bf6835cba7299ec8421
2021-08-22 23:56:07 -07:00
7535199f78
SWDEV-2 - Change OpenCL version number from 3336 to 3337
2021-08-22 23:56:07 -07:00
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
66ccdf6fb5
SWDEV-2 - Change OpenCL version number from 3335 to 3336
2021-08-22 23:56:07 -07:00
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
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
56d9240da4
SWDEV-2 - Change OpenCL version number from 3334 to 3335
2021-08-22 23:56:07 -07:00
970bc2c4f5
SWDEV-273235 - Restore missing LinuxPro option
...
Change-Id: Iccc0206f3f2c5b3c03f6ed313537f0f364a4ca29
2021-08-22 23:56:07 -07:00
ed7675ce51
SWDEV-2 - Change OpenCL version number from 3333 to 3334
2021-08-22 23:56:07 -07:00
d96481fb36
SWDEV-293742 - Update copyright end year VDI repo
...
Change-Id: I69d2fea4a7a43adf96ccea794270e4af991c5261
2021-08-22 23:56:07 -07:00
b065eb2d00
SWDEV-2 - Change OpenCL version number from 3332 to 3333
2021-08-22 23:56:07 -07:00
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
f4032401cf
SWDEV-289378 - Avoid CPU TS overwrite if GPU TS is available
...
Change-Id: I444ec284669b6a6fff31182e213b47c562c90192
2021-08-22 23:56:07 -07:00
4fd506cfe1
SWDEV-289378 - Avoid CPU TS overwrite if GPU TS is available
...
Change-Id: I2fc1a43c048b4fa1e42f27c4cf5c72fc7ae84e9c
2021-08-22 23:56:07 -07:00
50a50c66b9
SWDEV-2 - Change OpenCL version number from 3331 to 3332
2021-08-22 23:56:07 -07:00
ed0e7f659d
SWDEV-286322 - Add .gitattribute
...
Change-Id: I4ae4c4498765f10c98bb5f2443a083463b0e25af
2021-08-22 23:56:07 -07:00
1d9bf4f0b9
SWDEV-2 - Change OpenCL version number from 3330 to 3331
2021-08-22 23:56:07 -07:00
c11c02f2c7
SWDEV-285333 - Introduce Address sanitizer hostcall service
...
Change-Id: Id29aacd09d0a9934a027446c57c7095804e1a454
2021-08-22 23:56:07 -07:00
ffa29fad01
SWDEV-2 - Change OpenCL version number from 3329 to 3330
2021-08-22 23:56:07 -07:00
6ab8dcc682
SWDEV-292018 - Avoid marker if queue is empty
...
Change-Id: I40a42d67d2c911d2c9a0bf425f36bc795f9539c0
2021-08-22 23:56:07 -07:00
f6c00765e7
SWDEV-274815 - [PAL] Navi24 support
...
Change-Id: I934797bda471618c3f69484a1552b37345ae638b
2021-08-22 23:56:07 -07:00
a58ef5dd8f
SWDEV-2 - Change OpenCL version number from 3328 to 3329
2021-08-22 23:56:07 -07:00
b793811ef6
SWDEV-287088 - Workaround VM page fault on Windows
...
Some chunk memory are not guaranteed to be resident during
initial allocation. Use CPDMA to force resident.
Change-Id: If1a2da3e75f136caaa4c7a29d8f604d6af2639fa
2021-08-22 23:56:07 -07:00
20e2153e8b
SWDEV-290901 - update ROC_ACTIVE_WAIT_TIMEOUT to 50us
...
Change-Id: Iba2f2bb882c4786a432a523cb0954761e5359e7f
2021-08-22 23:56:07 -07:00
4e8c55829b
SWDEV-2 - Change OpenCL version number from 3327 to 3328
2021-08-22 23:56:07 -07:00
ce8dad2ecc
SWDEV-290160 - Switch to global HSA signals
...
Runtime can't assign internal HSA signals for HIP events, because
HIP application can destroy the HIP stream or signal reuse may
occur internally. Switch to global HSA signals for HIP events.
Change-Id: Ieaea2d6b039e492b2e7c5112782a8f4e601e50a1
2021-08-22 23:56:07 -07:00
b5b1ccc990
SWDEV-290122 - OpenGL tests fails with CL_MEM_ALLOCATION_ERROR
...
Change-Id: I34d7063f05dd46c32cf59a88c455691ba5099679
2021-08-22 23:56:07 -07:00
2dd18dc004
SWDEV-2 - Change OpenCL version number from 3326 to 3327
2021-08-22 23:56:07 -07:00
8e08880cc3
SWDEV-247372 - Add logging for debug
...
Change-Id: Id5a27034005a7deba37072d8a4c6f250104a96c8
2021-08-22 23:56:07 -07:00
82e572c23f
SWDEV-2 - Change OpenCL version number from 3325 to 3326
2021-08-22 23:56:07 -07:00
133287f31f
SWDEV-240806 - Release resources in Command::terminate for HIP
...
We do not want to release resources during setStatus in HIP because of Graphs
Change-Id: Idc7b188ab5f8be6975ea91005dd2bbf177401f8c
2021-08-22 23:56:07 -07:00
c49f1069ab
SWDEV-290160 - Don't send notification for batch markers
...
Batch marker already has a barrier with HSA signal callback
Change-Id: I69fc63d72320c2e9cc2d2e59ebd3f07c0bd0e3b5
2021-08-22 23:56:07 -07:00
83ca0821af
SWDEV-2 - Change OpenCL version number from 3324 to 3325
2021-08-22 23:56:07 -07:00
b2a1dc26ba
SWDEV-286446 - This patch enables stream operations on vega10, vega20, MI100 and MI200
...
Change-Id: I6f07036d8ee6e4c6b55196a13288f8107488d824
2021-08-22 23:56:07 -07:00
eaf0da8af3
SWDEV-2 - Change OpenCL version number from 3323 to 3324
2021-08-22 23:56:07 -07:00
d3213eca90
SWDEV-247372 - Reset hasPendingDispatch
...
Reset hasPendingDispatch_ if we insert barrier for time marker.
Change-Id: Id038fd4e1c910c0a657978fee00630e49c372321
2021-08-22 23:56:07 -07:00
b5528c8121
SWDEV-2 - Change OpenCL version number from 3322 to 3323
2021-08-22 23:56:07 -07:00
fe2d7424e5
SWDEV-290474 - [Lnx][VanGogh] Add VanGogh support
...
Signed-off-by: Aaron Liu <aaron.liu@amd.com >
Reviewed-by: Christophe Paquot <christophe.paquot@amd.com >
Change-Id: Iff0253a181bbfc1984304014a9e3b542b2556635
2021-08-22 23:56:07 -07:00
a1629cad26
SWDEV-290371 - Add lock protection for signal
...
Add lock protection for signal processing
If signal is reused, then disable reference to it from HIP
Increase the pool signal size to 32
Change-Id: I7d529b35910f83ce577c9eca6d3386759611ccc0
2021-08-22 23:56:07 -07:00
0af6ba9428
SWDEV-286092 - Use Barrier Header for event
...
Change-Id: I9701fbab587e2ea31e58449e8c8b07341a7aa161
2021-08-22 23:56:07 -07:00
b818301d53
SWDEV-290306 - [LNX][Navi24][mainline]clinfo test failed on Navi24
...
Add Navi 24 support
Change-Id: I7343384cf6fb8c532321e57e202c196ef054f459
2021-08-22 23:56:07 -07:00
b416ad7b9d
SWDEV-247372 - Active wait timeout env var
...
- Create an env var ROC_ACTIVE_WAIT_TIMEOUT to set active wait timeout
- Record profiling informaion if marker_ts_ property is valid.
Change-Id: If0d8aec8d9b0715027cf0f7c3dc8a4c722a6bae6
2021-08-22 23:56:07 -07:00
3b9b874947
SWDEV-2 - Change OpenCL version number from 3321 to 3322
2021-08-22 23:56:07 -07:00
8b22111f4b
SWDEV-289250 - Should return a nullptr for PAL so we can assume it's a host ptr
...
Change-Id: I530eb39104bbe727c3e38186f6db4e64285b3fc8
2021-08-22 23:56:07 -07:00
d13581efa7
SWDEV-276396 - Implement hipDeviceReset
...
Add a Purge function to MemObjMap
Change-Id: Iac51dfda9a7b7c45f2f4a0dc35f7a623121aba1a
2021-08-22 23:56:07 -07:00
85c70a7495
SWDEV-284671 - Add HW event wait to improve hipDeviceSynchronize
...
If AMD event contains a reference to a HW event, then runtime
could check/wait for HW event. CPU status update will occur later
after HSA signal callback, but it's not important for the result.
Change-Id: I591391a953bbdba6a25ac07e2cd98aeb17cd4596
2021-08-22 23:56:07 -07:00
5fdf5d05df
SWDEV-2 - Change OpenCL version number from 3320 to 3321
2021-08-22 23:56:07 -07:00
0b1481d4f1
SWDEV-289548 - [PAL] Revive Raven 2 support
...
Revert back to using the Raven (gfx902) target ID for Raven 2 (gfx909).
This is due to the HSAIL compiler not supporting gfx909.
In theory there should be no issue with running Raven isa on Raven 2.
Change-Id: I425edebc99075799eda5522fad231b8fb3184873
2021-08-22 23:56:07 -07:00
957b73c39e
SWDEV-2 - Change OpenCL version number from 3319 to 3320
2021-08-22 23:56:07 -07:00
9d0846e732
SWDEV-286092 - Enable handler for marker always
...
For DD, send a NOP packet so that we leverage the handler to indicate
completion.
Change-Id: Ie57ea0124a8497d39cc49da1c4575c2cd86b9319
2021-08-22 23:56:07 -07:00
German Andryeyev
Chauncey Hui
Sourabh Betigeri
Vladislav Sytchenko
agunashe
Saleel Kudchadker
jujiang
pvellien
Jason Tang
Anusha GodavarthySurya
Alex Xie
Christophe Paquot
Aaron Liu
Arya.Rafii