Grafico dei commit

41023 Commit

Autore SHA1 Messaggio Data
Galantsev, Dmitrii 89a495e493 Profiler - Remove rocprofiler-v1 remnants
Also force unset HSA_TOOLS_LIB so it doesn't break rocprofiler-sdk

Signed-off-by: Galantsev, Dmitrii <dmitrii.galantsev@amd.com>


[ROCm/rdc commit: e73eaf8115]
2025-06-27 13:15:52 -05:00
vedithal-amd 86e243201e Fix SPI block counter limit (#780)
* Fix SPI counter collection limit

* Update counter collection limits from aqlprofile

* Remove special handling for MI 350 SPI pipe counters

[ROCm/rocprofiler-compute commit: 6e1bbb5efb]
2025-06-27 14:07:56 -04:00
vedithal-amd 6e1bbb5efb Fix SPI block counter limit (#780)
* Fix SPI counter collection limit

* Update counter collection limits from aqlprofile

* Remove special handling for MI 350 SPI pipe counters
2025-06-27 14:07:56 -04:00
Xie, AlexBin ef26fcdbd2 SWDEV-530767 ocltst GL test work with GL context on 2nd GPU (#324)
Change-Id: Ia3dbc661b3b9b1de71a632969707318f208131cd
2025-06-27 12:25:23 -04:00
Xie, AlexBin 592c25e936 SWDEV-540176 - deb and rpm package include OpenCL config files (#615) 2025-06-27 11:59:24 -04:00
Lytovchenko, Danylo c8571baa23 SWDEV-123456 - add correct line-by-line clang format script (#215) 2025-06-27 17:47:31 +02:00
Lytovchenko, Danylo 1f14151706 SWDEV-123456 - add correct line-by-line clang format script (#360) 2025-06-27 17:47:21 +02:00
Lytovchenko, Danylo d9ec8a0977 SWDEV-123456 - add correct line-by-line clang format script (#19) 2025-06-27 17:47:11 +02:00
Pranjal Swarup 0497b7934f Update RCCL-tests in examples folder (#261)
- Create a local copy for ROCm/rccl-tests for our examples.
- Update argument parsing to no longer use getopt_long.
- Workaround for Dyninst instrumentation.

---------

Co-authored-by: David Galiffi <David.Galiffi@amd.com>

[ROCm/rocprofiler-systems commit: 4e5029221b]
2025-06-27 11:44:13 -04:00
Pranjal Swarup 4e5029221b Update RCCL-tests in examples folder (#261)
- Create a local copy for ROCm/rccl-tests for our examples.
- Update argument parsing to no longer use getopt_long.
- Workaround for Dyninst instrumentation.

---------

Co-authored-by: David Galiffi <David.Galiffi@amd.com>
2025-06-27 11:44:13 -04:00
Honglei Huang d874b8003a rocr/driver: add SetTrapHandler API to driver interface
This commit introduces a new SetTrapHandler API to the driver interface

- Implemented SetTrapHandler in KfdDriver to set trap handlers using
  hsaKmtSetTrapHandler.
- Added a stub implementation of SetTrapHandler in XdnaDriver that returns
  HSA_STATUS_ERROR.
- Updated the driver interface in driver.h to include the new SetTrapHandler
  method.
- Modified GpuAgent to use driver().SetTrapHandler instead of directly calling
  hsaKmtSetTrapHandler.

Signed-off-by: Honglei Huang <Honglei1.Huang@amd.com>
2025-06-27 23:32:53 +08:00
Honglei Huang 4fea8ea1fd rocr/driver: add SetTrapHandler API to driver interface
This commit introduces a new SetTrapHandler API to the driver interface

- Implemented SetTrapHandler in KfdDriver to set trap handlers using
  hsaKmtSetTrapHandler.
- Added a stub implementation of SetTrapHandler in XdnaDriver that returns
  HSA_STATUS_ERROR.
- Updated the driver interface in driver.h to include the new SetTrapHandler
  method.
- Modified GpuAgent to use driver().SetTrapHandler instead of directly calling
  hsaKmtSetTrapHandler.

Signed-off-by: Honglei Huang <Honglei1.Huang@amd.com>


[ROCm/ROCR-Runtime commit: d874b8003a]
2025-06-27 23:32:53 +08:00
Bhardwaj, Gopesh 639064b28c SWDEV-539836 Do not parse private/internal members (#56)
[ROCm/roctracer commit: 074d9d95ec]
2025-06-27 20:47:30 +05:30
Bhardwaj, Gopesh 074d9d95ec SWDEV-539836 Do not parse private/internal members (#56) 2025-06-27 20:47:30 +05:30
Bhardwaj, Gopesh 03b8988d9b SWDEV-539836 Do not parse private/internal members (#71)
[ROCm/rocprofiler commit: 93e0c4a17c]
2025-06-27 20:46:14 +05:30
Bhardwaj, Gopesh 93e0c4a17c SWDEV-539836 Do not parse private/internal members (#71) 2025-06-27 20:46:14 +05:30
Guan, Zichuan 51508e0bef Fix memory leak in opengl interop (#541)
Signed-off-by: zichguan-amd <zichuan.guan@amd.com>
2025-06-27 09:51:18 -04:00
Belton-Schure, Aidan 5e77c58bd0 SWDEV-536813 - Make alignment 16 for special cases (#609) 2025-06-27 14:20:16 +05:30
Lin, Qun b584fc8cd1 SWDEV-508869 - Replace asicRevision with gfxip triple in paldevice (#601)
asicRevision is not unique in pal path now, use gfxip triple to match isa is more straight forward in pal path.
2025-06-27 10:09:21 +08:00
Lin, Qun 9699cc3864 SWDEV-508869 - Fix Linux build error for HIP on PAL (#176) 2025-06-27 07:51:22 +08:00
Luu, Jonathan a2dafbeacf SWDEV-531400_SYMLINK remove SYMLINK (#525)
Co-authored-by: Jonathan Luu <jonatluu@amd.com>
2025-06-26 15:53:39 -04:00
Luu, Jonathan c64d56195f SWDEV-531400 - Remove file reorganization backward compatibility (clr hip) (#472)
* SWDEV-531400 Remove file reorganization backward compatibility (clr hip)

* SWDEV-531400 remove backwards compatibility for opencl

* SWDEV-531400 remove header_template.hpp.in

---------

Co-authored-by: Jonathan Luu <jonatluu@amd.com>
2025-06-26 15:53:11 -04:00
Fei Zheng 2ffaf5b453 Documentation update for FP8 on MI300 (#766)
[ROCm/rocprofiler-compute commit: f5bc717fe1]
2025-06-26 13:35:36 -06:00
Fei Zheng f5bc717fe1 Documentation update for FP8 on MI300 (#766) 2025-06-26 13:35:36 -06:00
Kandula, Venkateshwar reddy 8f5d00ca5d [SDK] Add gfx950 targets for tests and samples (#399)
* add gfx950 targets.

* add gfx950 targets to ci workflows.

* Format.

---------

Co-authored-by: Venkateshwar Reddy Kandula <vkandula@amd.com>
Co-authored-by: Vaddireddy, Sushma <Sushma.Vaddireddy@amd.com>

[ROCm/rocprofiler-sdk commit: 375866383b]
2025-06-26 14:25:08 -05:00
Kandula, Venkateshwar reddy 375866383b [SDK] Add gfx950 targets for tests and samples (#399)
* add gfx950 targets.

* add gfx950 targets to ci workflows.

* Format.

---------

Co-authored-by: Venkateshwar Reddy Kandula <vkandula@amd.com>
Co-authored-by: Vaddireddy, Sushma <Sushma.Vaddireddy@amd.com>
2025-06-26 14:25:08 -05:00
Trowbridge, Ian b461671093 Modified perfetto output for HIP stream display (#431)
* Modified perfetto output for HIP stream display

* Moved stream_map file location and changed perfetto output names Private_Segment_Size and Group_Segment_Size to Scratch_Size and LDS_Block_Size respectively

* Used const_cast to remove const modifier on void*

* Reverted stream_map changes, now using tool_metadata map to track mapping between stream ptrs and stream IDs

* Removed buffer tracing args in perfetto, added tool_...hip buffer record struct that stores the HIP stream ID for display purposes

* Updated rocpd perfetto.cpp to reflect stream changes. Still need to add vgpr values and stream ID for HIP API

* Changes pass-by const reference to pass-by const value

[ROCm/rocprofiler-sdk commit: 1f8b8c5e9f]
2025-06-26 14:22:50 -05:00
Trowbridge, Ian 1f8b8c5e9f Modified perfetto output for HIP stream display (#431)
* Modified perfetto output for HIP stream display

* Moved stream_map file location and changed perfetto output names Private_Segment_Size and Group_Segment_Size to Scratch_Size and LDS_Block_Size respectively

* Used const_cast to remove const modifier on void*

* Reverted stream_map changes, now using tool_metadata map to track mapping between stream ptrs and stream IDs

* Removed buffer tracing args in perfetto, added tool_...hip buffer record struct that stores the HIP stream ID for display purposes

* Updated rocpd perfetto.cpp to reflect stream changes. Still need to add vgpr values and stream ID for HIP API

* Changes pass-by const reference to pass-by const value
2025-06-26 14:22:50 -05:00
Ramakrishnan, Ranjith 25094a2c08 SWDEV-539684 - Package dependency updated with hsa-rocr (#130)
hsa-rocr was missing in the dependency list of aqlprofile package
Updated dependency for ASAN and aqlprofile test package as well

Co-authored-by: raramakr_amdeng <raramakr@amd.com>

[ROCm/aqlprofile commit: eebb229d08]
2025-06-26 11:34:49 -07:00
Ramakrishnan, Ranjith eebb229d08 SWDEV-539684 - Package dependency updated with hsa-rocr (#130)
hsa-rocr was missing in the dependency list of aqlprofile package
Updated dependency for ASAN and aqlprofile test package as well

Co-authored-by: raramakr_amdeng <raramakr@amd.com>
2025-06-26 11:34:49 -07:00
Kuricheti, Mythreya bde07e7baa [SDK] KFD new events API (#321)
* Remove page-migration

* Add KFD events API

* Address review comments

* Move assert checks

* Update enum-string utils

* Update codeowners

* Update KFD header

* Add perfetto category

[ROCm/rocprofiler-sdk commit: 8a461afe20]
2025-06-26 13:28:45 -05:00
Kuricheti, Mythreya 8a461afe20 [SDK] KFD new events API (#321)
* Remove page-migration

* Add KFD events API

* Address review comments

* Move assert checks

* Update enum-string utils

* Update codeowners

* Update KFD header

* Add perfetto category
2025-06-26 13:28:45 -05:00
Sang, Tao f4d78d427c SWDEV-539399 - Support ROCCLR_MEM_HSA_CONTIGUOUS (#610)
Fix missing support of ROCCLR_MEM_HSA_CONTIGUOUS in
hipExtMallocWithFlags().
2025-06-26 14:05:23 -04:00
vedithal-amd 1d59cbb06d Add support for MI 100 with rocprofiler-sdk (#768)
* Add custom rocprofiler-sdk counter definitions file for MI 100

* Update CHANGELOG to mention that accumulation counters will not be
  collected when profiling on MI 100 using rocprofiler-sdk/rocprofv3

* Migrate accum_counters.yaml to code

[ROCm/rocprofiler-compute commit: a95a45d69a]
2025-06-26 09:03:18 -04:00
vedithal-amd a95a45d69a Add support for MI 100 with rocprofiler-sdk (#768)
* Add custom rocprofiler-sdk counter definitions file for MI 100

* Update CHANGELOG to mention that accumulation counters will not be
  collected when profiling on MI 100 using rocprofiler-sdk/rocprofv3

* Migrate accum_counters.yaml to code
2025-06-26 09:03:18 -04:00
Lytovchenko, Danylo 2ec7b7fdb4 SWDEV-123456 - fix runners name (#208) 2025-06-26 12:15:49 +02:00
Lytovchenko, Danylo 1992d81122 SWDEV-123456 - fix runners names (#18) 2025-06-26 12:15:39 +02:00
Lytovchenko, Danylo c9ce31fb24 SWDEV-123456 - fix runners name (#351) 2025-06-26 12:15:36 +02:00
Jiang, Julia 8eca6453dc SWDEV-461599 - scrub HCC in hip documents (#178) 2025-06-26 15:06:31 +05:30
Jiang, Julia b5cd8321d3 SWDEV-461599 - scrub HCC in clr documents (#569) 2025-06-26 15:05:59 +05:30
Sicarov, Dragoslav a4631b5700 SWDEV-533232 Add num_threads API in cooperative_groups (#437)
* Add num_threads API in cooperative_groups
* Reimplementsize API as its alias.
* Update changelog
2025-06-26 15:05:17 +05:30
Arandjelovic, Marko 349b83c1f6 SWDEV-512344 - Allow unmapping of only complete subbuffers (#608)
* Do not allow partial unmapping
* Add check to prevent out of bounds unmap
* Improve code quality
* Use getOrigin instead of getOffset
2025-06-26 15:01:33 +05:30
Lytovchenko, Danylo 704fea29cf SWDEV-123456 - use explicit PR head SHA for clang-format (#623)
* SWDEV-123456 - use explicit PR head SHA for clang-format

* SWDEV-123456 - set new runners name
2025-06-26 10:46:02 +02:00
Honglei Huang dee5bdc679 rocr: replace direct libhsakmt calls with driver interfaces
Replace direct hsakmt API calls with calls through the driver abstraction layer
in queue management related functions. This includes:
- CreateQueue/DestroyQueue operations
- Queue update and GWS allocation
- CU masking configuration

Also update the corresponding error status types from HSAKMT_STATUS to
hsa_status_t and adjust error handling accordingly.

Signed-off-by: Honglei Huang <Honglei1.Huang@amd.com>
2025-06-26 15:53:01 +08:00
Honglei Huang 5e7fd3b5ba rocr: replace direct libhsakmt calls with driver interfaces
Replace direct hsakmt API calls with calls through the driver abstraction layer
in queue management related functions. This includes:
- CreateQueue/DestroyQueue operations
- Queue update and GWS allocation
- CU masking configuration

Also update the corresponding error status types from HSAKMT_STATUS to
hsa_status_t and adjust error handling accordingly.

Signed-off-by: Honglei Huang <Honglei1.Huang@amd.com>


[ROCm/ROCR-Runtime commit: dee5bdc679]
2025-06-26 15:53:01 +08:00
Honglei Huang 046591419f rocr: use driver interface for memory and cache properties query
Replace direct libhsakmt calls with driver interface methods
in GpuAgent initialization:
- Replace hsaKmtGetNodeMemoryProperties with driver().GetMemoryProperties
- Replace hsaKmtGetNodeCacheProperties with driver().GetCacheProperties

Signed-off-by: Honglei Huang <Honglei1.Huang@amd.com>
2025-06-26 15:53:01 +08:00
Honglei Huang 75a7da05be rocr: use driver interface for memory and cache properties query
Replace direct libhsakmt calls with driver interface methods
in GpuAgent initialization:
- Replace hsaKmtGetNodeMemoryProperties with driver().GetMemoryProperties
- Replace hsaKmtGetNodeCacheProperties with driver().GetCacheProperties

Signed-off-by: Honglei Huang <Honglei1.Huang@amd.com>


[ROCm/ROCR-Runtime commit: 046591419f]
2025-06-26 15:53:01 +08:00
Honglei Huang ffa07e28e7 rocr: remove unused agent properties reference in scratch initialization
The agent properties variable `agent_props` was declared but never used
in the `InitScratchSRD()` function. Which casued compile warning:

runtime/core/runtime/amd_aql_queue.cpp:1880:15: warning:
unused variable ‘agent_props’ [-Wunused-variable]
 1880 |   const auto& agent_props = agent_->properties();

No functional changes, purely a code cleanup commit.
2025-06-26 13:05:40 +08:00
Honglei Huang 97992b809f rocr: remove unused agent properties reference in scratch initialization
The agent properties variable `agent_props` was declared but never used
in the `InitScratchSRD()` function. Which casued compile warning:

runtime/core/runtime/amd_aql_queue.cpp:1880:15: warning:
unused variable ‘agent_props’ [-Wunused-variable]
 1880 |   const auto& agent_props = agent_->properties();

No functional changes, purely a code cleanup commit.


[ROCm/ROCR-Runtime commit: ffa07e28e7]
2025-06-26 13:05:40 +08:00
Tony Gutierrez 1a339feb1f rocr: Move OpenSMI call to Driver 2025-06-25 15:53:02 -07:00