Commit Graph

37726 Commits

Author SHA1 Message Date
Konstantin Zhuravlyov dd4378611a SWDEV-341212 - HIP header changes for supporting SPIR-V
This removes almost all uses of the deprecated
__AMDGCN_WAVEFRONT_SIZE macro, which is unavailable
when targeting SPIR-V, and adds a SPIR-V compatible
formulation of warpSize (which should end up as the
sole definition of warpSize once we remove support
for treating it as a compile time constant). It
is incomplete in that the cooperative_groups
implementation will need additional surgery.

Squashed commit of the following:

commit 6840826c3fec8516857dc4f2092d84358550f588
Author: Alex Voicu <alexandru.voicu@amd.com>
Date:   Fri Dec 6 23:36:32 2024 +0000

    Add deprecation warning for constexpr uses of `warpSize`.

commit a72307a7353034c2de53fd164e016967945fd0d1
Author: Alex Voicu <alexandru.voicu@amd.com>
Date:   Fri Dec 6 23:12:14 2024 +0000

    Prepare HIP RT for SPIR-V.

commit 5e40dd746ac4f8c93b521ef048ff9d494905ba95
Author: Alex Voicu <alexandru.voicu@amd.com>
Date:   Fri Dec 6 22:46:05 2024 +0000

    Revert stale change.

commit 231fe91c53dba4cabd832fc84eaa6ddb402271a0
Merge: a48905ec9 78f62d323
Author: Alex Voicu <alexandru.voicu@amd.com>
Date:   Fri Dec 6 22:37:24 2024 +0000

    Merge branch 'amd-staging' of https://github.com/ROCm/clr into amd-staging

commit a48905ec9cfe0e017cc64943195be82b530117d7
Author: Alex Voicu <alexandru.voicu@amd.com>
Date:   Tue Sep 17 03:14:56 2024 +0100

    Add scaffolding for SPIR-V support.

Change-Id: I2e84bbe90df58a5f9a8709b619905f04fa5b96dc
2025-01-20 08:42:24 -05:00
Jatin Chaudhary 6a5d19059d SWDEV-341217 - Initial work to use SPIRV in HIP
Change-Id: If5c09b5e86b498e7ac5eb05adf28cb7a1fac8101
2025-01-20 03:54:23 -05:00
Trowbridge, Ian 3e1b8ba4ec rocDecode API Tracing Support (#49)
* rocDecode API Tracing support

* Test bin file added to rocdecode. Need to add validate python methods

* Added option to not make rocDecode tests

* Added rocdecode and rocprofv3 tests

* Added csv test

* Address PR comments. Changed tests to use built-in rocstreambit decoder to remove ffmpeg dependancy. Changed cmake option to disbale tests rather than not build them. Tests work locally, but will fail until rocDecode is built with tracing enabled on CI

* Add option to avoid building rocdecode tests

* Added option to avoid building rocdecode bin file

* Merge conflict error

* CMake files changed in response to review comments. Attempting to implement callbacks.

* Turned off test building for rocdecode

* Minor fixes for review comments

* Review comments

* Updated formatting

* Document changes and format.hpp reversion. Need to remove iterate args support for now for later update.

* Remove iterate args support

* Remove iterate-args

* enforce abi versioning in macro if

* Fix doc error

* removed spaces to fix indentation error

---------

Co-authored-by: Madsen, Jonathan <Jonathan.Madsen@amd.com>

[ROCm/rocprofiler-sdk commit: e307b89ca4]
2025-01-17 14:42:25 -08:00
Trowbridge, Ian e307b89ca4 rocDecode API Tracing Support (#49)
* rocDecode API Tracing support

* Test bin file added to rocdecode. Need to add validate python methods

* Added option to not make rocDecode tests

* Added rocdecode and rocprofv3 tests

* Added csv test

* Address PR comments. Changed tests to use built-in rocstreambit decoder to remove ffmpeg dependancy. Changed cmake option to disbale tests rather than not build them. Tests work locally, but will fail until rocDecode is built with tracing enabled on CI

* Add option to avoid building rocdecode tests

* Added option to avoid building rocdecode bin file

* Merge conflict error

* CMake files changed in response to review comments. Attempting to implement callbacks.

* Turned off test building for rocdecode

* Minor fixes for review comments

* Review comments

* Updated formatting

* Document changes and format.hpp reversion. Need to remove iterate args support for now for later update.

* Remove iterate args support

* Remove iterate-args

* enforce abi versioning in macro if

* Fix doc error

* removed spaces to fix indentation error

---------

Co-authored-by: Madsen, Jonathan <Jonathan.Madsen@amd.com>
2025-01-17 14:42:25 -08:00
Baraldi, Giovanni 69d94c65a8 SWDEV-478762+FEAT-62196: Fix crash on AQL replay (#104)
* SWDEV-478762: Fix crash on replay

* Fix iteration range

* Format

* Refactor

* Addressing review comments

* Address review comments

* Formatting

* Format

* Refactor

---------

Co-authored-by: Giovanni Baraldi <gbaraldi@amd.com>

[ROCm/rocprofiler-sdk commit: 1f01526eed]
2025-01-17 12:23:48 -06:00
Baraldi, Giovanni 1f01526eed SWDEV-478762+FEAT-62196: Fix crash on AQL replay (#104)
* SWDEV-478762: Fix crash on replay

* Fix iteration range

* Format

* Refactor

* Addressing review comments

* Address review comments

* Formatting

* Format

* Refactor

---------

Co-authored-by: Giovanni Baraldi <gbaraldi@amd.com>
2025-01-17 12:23:48 -06:00
Jaydeep Patel 1aa8383b09 SWDEV-509664 - Specify type explicitly.
Change-Id: Ia0c0478682fa15eae7a31a2360310f08151716d4
2025-01-17 13:09:48 -05:00
Mallya, Ameya Keshava e2520ad547 Fixed Workflow for updated KWS structure
[ROCm/rocm_smi_lib commit: aefc865bf4]
2025-01-17 08:26:52 -08:00
Mallya, Ameya Keshava aefc865bf4 Fixed Workflow for updated KWS structure 2025-01-17 08:26:52 -08:00
Mallya, Ameya Keshava 047f6edc90 Fixed Workflow for updated KWS structure
[ROCm/rocprofiler-register commit: 164eda5231]
2025-01-17 08:25:42 -08:00
Mallya, Ameya Keshava 164eda5231 Fixed Workflow for updated KWS structure 2025-01-17 08:25:42 -08:00
Mallya, Ameya Keshava 1142cd1a88 Added KWS check
[ROCm/roctracer commit: f8189fd60d]
2025-01-17 08:23:51 -08:00
Mallya, Ameya Keshava f8189fd60d Added KWS check 2025-01-17 08:23:51 -08:00
Mallya, Ameya Keshava 09936e6937 Added KWS check 2025-01-17 08:22:53 -08:00
Mallya, Ameya Keshava 512d621ff0 Added KWS check
[ROCm/rocprofiler commit: 09936e6937]
2025-01-17 08:22:53 -08:00
Mallya, Ameya Keshava 0490b1c925 Fixed Workflow for updated KWS structure 2025-01-17 08:21:11 -08:00
Mallya, Ameya Keshava 7267692f1b Fixed Workflow for updated KWS structure
[ROCm/rdc commit: 0490b1c925]
2025-01-17 08:21:11 -08:00
Mallya, Ameya Keshava eaaeafbfa4 Fixed Workflow for updated KWS structure
[ROCm/rocprofiler-sdk commit: c5140c83a5]
2025-01-17 08:15:36 -08:00
Mallya, Ameya Keshava c5140c83a5 Fixed Workflow for updated KWS structure 2025-01-17 08:15:36 -08:00
Julia Jiang fe5c68d8a3 SWDEV-509295 - Update changelog with newly added HIP APIs for 6.4
Change-Id: I6052e3bf4f17d1fec23e6cc835aa2526ee0bc48c
2025-01-17 10:13:11 -05:00
Julia Jiang f497b79111 SWDEV-509295 - Merging changelog from 6.3.2 into amd-staging for 6.4
Change-Id: I0cd56b44402e82499616e961212abd2b3569c164
2025-01-17 10:12:44 -05:00
Marko Arandjelovic 08341ee719 SWDEV-509010 - Add missing CHECK_IMAGE_SUPPORT
Change-Id: I87c7925c0fbb7b8b9c1ecbeaa0a572f744f3a6bc
2025-01-17 08:14:22 -05:00
Branislav Brzak 3fd46a3783 SWDEV-508743 - [6.4 Preview] Add ROCm 7.0 breaking change fields
Change-Id: I07bff42731e74a4c409505cf8981342e22ce26be
2025-01-17 06:25:27 -05:00
Michael Xie b1f9f86543 SWDEV-494221 - Remove unnecessary hipEventRecord
- Removed unnecessary hipEventRecord and fixed time calculation in
  hipPerfDispatchSpeed.cc where it was off by a factor of 1,000.

Change-Id: If538e1d236cf0e6d3c69caf7af53c9095d812ad6
2025-01-16 11:45:20 -05:00
Rambabu Swargam 274fb5d974 SWDEV-493295 - [catch2][dtest] Adding additional tests for hipMalloc
Change-Id: I600e77ac5d07d169c34090041d2663741f3d4882
2025-01-16 11:23:06 -05:00
Vladana Stojiljkovic 30cb2d0e67 SWDEV-498061 - Add capture support for hipModuleLaunchCooperativeKernel
Change-Id: I5ed188e046c680c2785b3952391f59ed1d0c21b8
2025-01-16 10:54:30 -05:00
Marko Arandjelovic db8527f655 SWDEV-489619 - Fix memcpy tests with capture stream enabled
- Added missing validation as graph node should not be created
 if parameters are invalid
 - Fix conversion of input params to graphNode params

Change-Id: I37ab04942b5fb2eb07386850cb7dbbf26f9ca967
2025-01-16 10:31:04 -05:00
Marko Arandjelovic c46f843b99 SWDEV-504084 - Make hipModuleGetFunction use the device the module is loaded on
If a module is loaded on one device, hipModuleGetFunction and other similar APIs should be able to run successfully from another device.

Change-Id: I96084cbd6c6dcf2a81019779a6ab1842ef2f35d1
2025-01-16 10:16:42 -05:00
Jakaraddi, Manjunath 324c57ede1 SWDEV-500520: Updated documentation for hang issue (#79)
* SWDEV-500520: Updated documentation for hang issue

* Avoid fatal error when invalid metric is found

* removing invalid metrics

* clang formatting

[ROCm/rocprofiler-sdk commit: dfee6489b1]
2025-01-16 02:14:22 -08:00
Jakaraddi, Manjunath dfee6489b1 SWDEV-500520: Updated documentation for hang issue (#79)
* SWDEV-500520: Updated documentation for hang issue

* Avoid fatal error when invalid metric is found

* removing invalid metrics

* clang formatting
2025-01-16 02:14:22 -08:00
Welton, Benjamin ee959cc591 [SWDEV-509659] Skip rocprof device counting tests if lacking permissions (#125)
* [SWDEV-509659] Skip rocprof device counting tests if lacking permissions

Skips non-intercept test if proper permissions are not obtained
(SYS_PERFMON). This should be the only test that fails due to permission
issues (others do not require the IOCTL to pass).

Regex match sample: https://regexr.com/8b29s

* Update source/lib/rocprofiler-sdk/counters/tests/CMakeLists.txt

Co-authored-by: Madsen, Jonathan <Jonathan.Madsen@amd.com>

* fix

* Update source/lib/rocprofiler-sdk/counters/tests/CMakeLists.txt

---------

Co-authored-by: Benjamin Welton <ben@amd.com>
Co-authored-by: Madsen, Jonathan <Jonathan.Madsen@amd.com>

[ROCm/rocprofiler-sdk commit: 536fbba627]
2025-01-16 01:51:06 -06:00
Welton, Benjamin 536fbba627 [SWDEV-509659] Skip rocprof device counting tests if lacking permissions (#125)
* [SWDEV-509659] Skip rocprof device counting tests if lacking permissions

Skips non-intercept test if proper permissions are not obtained
(SYS_PERFMON). This should be the only test that fails due to permission
issues (others do not require the IOCTL to pass).

Regex match sample: https://regexr.com/8b29s

* Update source/lib/rocprofiler-sdk/counters/tests/CMakeLists.txt

Co-authored-by: Madsen, Jonathan <Jonathan.Madsen@amd.com>

* fix

* Update source/lib/rocprofiler-sdk/counters/tests/CMakeLists.txt

---------

Co-authored-by: Benjamin Welton <ben@amd.com>
Co-authored-by: Madsen, Jonathan <Jonathan.Madsen@amd.com>
2025-01-16 01:51:06 -06:00
Welton, Benjamin 9a8b8bf905 Small debug print fix in ioctl.cpp (#120)
* Small debug print fix in ioctl.cpp

Fix debug print statement to print agent id.

* formatting

---------

Co-authored-by: Jonathan R. Madsen <jonathanrmadsen@gmail.com>

[ROCm/rocprofiler-sdk commit: 71dc203b0c]
2025-01-15 18:00:04 -08:00
Welton, Benjamin 71dc203b0c Small debug print fix in ioctl.cpp (#120)
* Small debug print fix in ioctl.cpp

Fix debug print statement to print agent id.

* formatting

---------

Co-authored-by: Jonathan R. Madsen <jonathanrmadsen@gmail.com>
2025-01-15 18:00:04 -08:00
Madsen, Jonathan baee324bfc Fix host function logging (#63)
Co-authored-by: Jonathan R. Madsen <jonathanrmadsen@gmail.com>

[ROCm/rocprofiler-sdk commit: fae4ad614c]
2025-01-15 19:54:35 -06:00
Madsen, Jonathan fae4ad614c Fix host function logging (#63)
Co-authored-by: Jonathan R. Madsen <jonathanrmadsen@gmail.com>
2025-01-15 19:54:35 -06:00
Madsen, Jonathan 3250a26c79 Split ABI checks for rocprofiler-sdk-roctx into separate file (#21)
* Split ABI checks for rocprofiler-sdk-roctx into separate file

* Update source/lib/rocprofiler-sdk-roctx/abi.cpp

Co-authored-by: Indic, Vladimir <Vladimir.Indic@amd.com>

* Update source/lib/rocprofiler-sdk-roctx/abi.cpp

Co-authored-by: Indic, Vladimir <Vladimir.Indic@amd.com>

* New line

---------

Co-authored-by: Jonathan R. Madsen <jonathanrmadsen@gmail.com>
Co-authored-by: Indic, Vladimir <Vladimir.Indic@amd.com>

[ROCm/rocprofiler-sdk commit: 1b7ab08ded]
2025-01-15 19:32:50 -06:00
Madsen, Jonathan 1b7ab08ded Split ABI checks for rocprofiler-sdk-roctx into separate file (#21)
* Split ABI checks for rocprofiler-sdk-roctx into separate file

* Update source/lib/rocprofiler-sdk-roctx/abi.cpp

Co-authored-by: Indic, Vladimir <Vladimir.Indic@amd.com>

* Update source/lib/rocprofiler-sdk-roctx/abi.cpp

Co-authored-by: Indic, Vladimir <Vladimir.Indic@amd.com>

* New line

---------

Co-authored-by: Jonathan R. Madsen <jonathanrmadsen@gmail.com>
Co-authored-by: Indic, Vladimir <Vladimir.Indic@amd.com>
2025-01-15 19:32:50 -06:00
Ioannis Assiouras 5e3a29078d SWDEV-505503 - Use internal device synchronize function in __hipUnregisterFatBinary
This is to avoid calling the HIP_INIT macro during the shutdown process.

Change-Id: I2e65f6e10491918a17445ee1e8ddd08286070358
2025-01-15 18:57:34 -05:00
Ioannis Assiouras 78c5e6e502 SWDEV-506983 - Added check for image support in Unit_hipTexRef[Get/Set]BorderColor_Negative
Change-Id: Ie2aead3b94d97917bdc0a57125e80dcfd1a60f28
2025-01-15 18:57:28 -05:00
Mallya, Ameya Keshava c687f9baa5 Add KWS Check (#9)
[ROCm/rocm_smi_lib commit: dcdaf7389e]
2025-01-15 12:05:09 -08:00
Mallya, Ameya Keshava dcdaf7389e Add KWS Check (#9) 2025-01-15 12:05:09 -08:00
agunashe 05b59788c6 SWDEV-504240 - linux: skip atomicMax tests for all ASICs
Change-Id: Ic7b37f0734f728c2ef21e7acd9f280039fbbe4b2
2025-01-15 14:38:13 -05:00
Mallya, Ameya Keshava 502a8386c6 Added KWS check
[ROCm/rocprofiler-register commit: 3bd980bff8]
2025-01-15 11:15:00 -08:00
Mallya, Ameya Keshava 3bd980bff8 Added KWS check 2025-01-15 11:15:00 -08:00
Mallya, Ameya Keshava 49b96ca627 Create kws-caller.yml
[ROCm/rocm_smi_lib commit: c6ce9a5aa0]
2025-01-15 11:12:25 -08:00
Mallya, Ameya Keshava c6ce9a5aa0 Create kws-caller.yml 2025-01-15 11:12:25 -08:00
Mallya, Ameya Keshava cadbf69b45 Added KWS check (#88) 2025-01-15 11:11:01 -08:00
Mallya, Ameya Keshava 4206250e61 Added KWS check (#88)
[ROCm/rdc commit: cadbf69b45]
2025-01-15 11:11:01 -08:00
Mallya, Ameya Keshava 8641afe3fe Changed branch to mainline
[ROCm/rocprofiler-sdk commit: 720763daac]
2025-01-15 11:08:20 -08:00