76333 Commits

Author SHA1 Message Date
guanyu12 723cc6be51 Merge amd-dev into amd-master 20240606
Signed-off-by: guanyu12 <guanyu12@amd.com>
Change-Id: I2b563e8fab6b26f80bd1ebac4c2e4b7c245a69e3
2024-06-06 16:46:10 +08:00
guanyu12 5e10a07fe2 Merge amd-dev into amd-master 20240606
Signed-off-by: guanyu12 <guanyu12@amd.com>
Change-Id: I2b563e8fab6b26f80bd1ebac4c2e4b7c245a69e3


[ROCm/amdsmi commit: 723cc6be51]
2024-06-06 16:46:10 +08:00
Ioannis Assiouras 0e023d1a0a SWDEV-463865 - symbol renamings to prevent conflicts in static build
Change-Id: Id7fbb638c1088c23df52fee877cd790d637b1ffb


[ROCm/clr commit: b8c2ac4de4]
2024-06-06 04:05:55 -04:00
Ioannis Assiouras b8c2ac4de4 SWDEV-463865 - symbol renamings to prevent conflicts in static build
Change-Id: Id7fbb638c1088c23df52fee877cd790d637b1ffb
2024-06-06 04:05:55 -04:00
Saleel Kudchadker 1c94521c1c SWDEV-463428 - Acquire correlation ID after clear
Change-Id: I472085178d5751f5e2c8a6dfe190b6b3249317f0


[ROCm/clr commit: ecff928284]
2024-06-06 03:49:01 -04:00
Saleel Kudchadker ecff928284 SWDEV-463428 - Acquire correlation ID after clear
Change-Id: I472085178d5751f5e2c8a6dfe190b6b3249317f0
2024-06-06 03:49:01 -04:00
Galantsev, Dmitrii 20ca2ce574 Fix rocprofiler plugin
- Replace non-working fields with working ones
    - remove CU_OCCUPANCY completely as it isn't well supported
- Fix rocprofiler initialization with shared_ptr and rdc_module_init
- Replace env var ROCPROFILER_METRICS_PATH with ROCP_METRICS
    - ROCPROFILER_METRICS_PATH is only relevant for rocprofv2
    - ROCP_METRICS is only relevant for rocprofv1 (which we are using)

Change-Id: I21e6fa3f0e1694c38f44ca0e5659d672559f7380
Signed-off-by: Galantsev, Dmitrii <dmitrii.galantsev@amd.com>
2024-06-06 01:51:39 -05:00
Galantsev, Dmitrii 29b86095ed Fix rocprofiler plugin
- Replace non-working fields with working ones
    - remove CU_OCCUPANCY completely as it isn't well supported
- Fix rocprofiler initialization with shared_ptr and rdc_module_init
- Replace env var ROCPROFILER_METRICS_PATH with ROCP_METRICS
    - ROCPROFILER_METRICS_PATH is only relevant for rocprofv2
    - ROCP_METRICS is only relevant for rocprofv1 (which we are using)

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


[ROCm/rdc commit: 20ca2ce574]
2024-06-06 01:51:39 -05:00
Galantsev, Dmitrii 23614524ac update_wrapper.sh - Fix grep command
Change-Id: I497fd0d1ac28adc0975b3ab0ea74ce30a9f84f29
Signed-off-by: Galantsev, Dmitrii <dmitrii.galantsev@amd.com>
2024-06-06 00:17:13 -04:00
Galantsev, Dmitrii e6a2a8db60 update_wrapper.sh - Fix grep command
Change-Id: I497fd0d1ac28adc0975b3ab0ea74ce30a9f84f29
Signed-off-by: Galantsev, Dmitrii <dmitrii.galantsev@amd.com>


[ROCm/amdsmi commit: 23614524ac]
2024-06-06 00:17:13 -04:00
Lakshmi Kumar 08f6417565 AV1: VA-API submission (#362)
* av1 va-api submission

* adding check for anchor_frames and current_diplay_picture

* check limits for memory errors

* review comment - remove unnecessary check

[ROCm/rocdecode commit: c70e98abb6]
2024-06-05 16:23:47 -04:00
Lakshmi Kumar c70e98abb6 AV1: VA-API submission (#362)
* av1 va-api submission

* adding check for anchor_frames and current_diplay_picture

* check limits for memory errors

* review comment - remove unnecessary check
2024-06-05 16:23:47 -04:00
Rahul Manocha 6eb8d8cb55 [SWDEV-438556][SWDEV-451646] - Fix for Warp vote catch tests
Change-Id: Icf9e0d488c4ba0267ce988b85d7b38478db9d1b8


[ROCm/hip-tests commit: e2ca8a03ff]
2024-06-05 14:32:03 -04:00
Rahul Manocha e2ca8a03ff [SWDEV-438556][SWDEV-451646] - Fix for Warp vote catch tests
Change-Id: Icf9e0d488c4ba0267ce988b85d7b38478db9d1b8
2024-06-05 14:32:03 -04:00
Bill(Shuzhou) Liu 4cf59c4edb Change the name of clear sram to run cleaner shader
The function is to clean the local data in LDS/GPRs. The clear sram
is misleading.

Change-Id: I0385e6d6348602fe0f347d17e48ed8983f7ceb87
2024-06-05 12:07:39 -05:00
Bill(Shuzhou) Liu b517f3c214 Change the name of clear sram to run cleaner shader
The function is to clean the local data in LDS/GPRs. The clear sram
is misleading.

Change-Id: I0385e6d6348602fe0f347d17e48ed8983f7ceb87


[ROCm/amdsmi commit: 4cf59c4edb]
2024-06-05 12:07:39 -05:00
gobhardw 1e69b3e2f6 SWDEV-465520: RHEL9 toolchain doesnt seem to support experimental filesystem
Change-Id: I6b1e7f42c49b1c7af412c0b68851724861c9970a
2024-06-05 12:50:48 -04:00
gobhardw a67f4fdd93 SWDEV-465520: RHEL9 toolchain doesnt seem to support experimental filesystem
Change-Id: I6b1e7f42c49b1c7af412c0b68851724861c9970a


[ROCm/rocprofiler commit: 1e69b3e2f6]
2024-06-05 12:50:48 -04:00
Jaydeep Patel 7d99f46d2b SWDEV-464788 - Let hipMallocPitch deduce type instead to specify explicit type.
Change-Id: Iab20c19531ee49088bfd03b289cd0a6cfe173385


[ROCm/hip commit: 006ce388de]
2024-06-05 16:05:41 +00:00
Jaydeep Patel 006ce388de SWDEV-464788 - Let hipMallocPitch deduce type instead to specify explicit type.
Change-Id: Iab20c19531ee49088bfd03b289cd0a6cfe173385
2024-06-05 16:05:41 +00:00
Giovanni LB 140f658820 SWDEV-464906: Swap read and stop packets in queue.cpp
Change-Id: I2dd33a71c0cbe69fe6c2cfaf523b9f8c6500093f
2024-06-05 09:11:59 -04:00
Giovanni LB 607cfb9ee1 SWDEV-464906: Swap read and stop packets in queue.cpp
Change-Id: I2dd33a71c0cbe69fe6c2cfaf523b9f8c6500093f


[ROCm/rocprofiler commit: 140f658820]
2024-06-05 09:11:59 -04:00
Benjamin Welton 29628c5bc5 Use fixed size array for serialization (#906)
Co-authored-by: Benjamin Welton <ben@amd.com>

[ROCm/rocprofiler-sdk commit: 2f3a8b05b3]
2024-06-05 02:02:01 -07:00
Benjamin Welton 2f3a8b05b3 Use fixed size array for serialization (#906)
Co-authored-by: Benjamin Welton <ben@amd.com>
2024-06-05 02:02:01 -07:00
Jaydeep Patel 47b1a7b98b SWDEV-465461 - Use command's queue instead as it might be changed while constructing memcpy command on MGPU.
Change-Id: Ia6ac40289e1eea320925203cbd52b30f3b64ad2b


[ROCm/clr commit: 774a10201f]
2024-06-05 06:47:49 +00:00
Jaydeep Patel 774a10201f SWDEV-465461 - Use command's queue instead as it might be changed while constructing memcpy command on MGPU.
Change-Id: Ia6ac40289e1eea320925203cbd52b30f3b64ad2b
2024-06-05 06:47:49 +00:00
amd-jmacaran 2c5c9e38db External CI: change supported branches
Change-Id: I3c3db1243d067720fd141eeb204d9b0b3e7a9fd6


[ROCm/rocminfo commit: 2bd32b0daf]
2024-06-05 01:51:43 -04:00
amd-jmacaran 2bd32b0daf External CI: change supported branches
Change-Id: I3c3db1243d067720fd141eeb204d9b0b3e7a9fd6
2024-06-05 01:51:43 -04:00
gobhardw 341b7b1f21 removing --kernel-trace from --sys-trace help
Change-Id: I14afd42d12bc3c2462040d5ba1f16765565fd662
2024-06-05 11:18:58 +05:30
gobhardw a95064a9a5 removing --kernel-trace from --sys-trace help
Change-Id: I14afd42d12bc3c2462040d5ba1f16765565fd662


[ROCm/rocprofiler commit: 341b7b1f21]
2024-06-05 11:18:58 +05:30
Galantsev, Dmitrii 07c414af5e Finalize the rocprofiler fields
Change-Id: I4ed1c4309f21bdcc7281d911663036caf5947182
Signed-off-by: Galantsev, Dmitrii <dmitrii.galantsev@amd.com>
2024-06-04 19:49:06 -05:00
Galantsev, Dmitrii c2a75bbe4c Finalize the rocprofiler fields
Change-Id: I4ed1c4309f21bdcc7281d911663036caf5947182
Signed-off-by: Galantsev, Dmitrii <dmitrii.galantsev@amd.com>


[ROCm/rdc commit: 07c414af5e]
2024-06-04 19:49:06 -05:00
saurabhAMD bdaf71070a Merge pull request #79 from saurabhAMD/rotating_tensor
Rotating tensor -R (default:off)

[ROCm/rccl-tests commit: 073d56f6e2]
2024-06-04 17:51:26 -05:00
saurabhAMD 073d56f6e2 Merge pull request #79 from saurabhAMD/rotating_tensor
Rotating tensor -R (default:off)
2024-06-04 17:51:26 -05:00
Gu, Wangfeng 28009e625b SWDEV-460019 - [OGLP][Nv2x] DaVinci Resolve Studio: Crash observed when editing in color tab
When CL-GL interop is used, a GL context are used by two or more threads at the same time, which causes race condition.

Solution:
Add lock when accessing GL functions during CL-GL interop.

Change-Id: I3a34da3cbdf74c401111cc4e3a04ad84cc52709e


[ROCm/clr commit: 0c6a952a90]
2024-06-04 16:35:44 -04:00
Gu, Wangfeng 0c6a952a90 SWDEV-460019 - [OGLP][Nv2x] DaVinci Resolve Studio: Crash observed when editing in color tab
When CL-GL interop is used, a GL context are used by two or more threads at the same time, which causes race condition.

Solution:
Add lock when accessing GL functions during CL-GL interop.

Change-Id: I3a34da3cbdf74c401111cc4e3a04ad84cc52709e
2024-06-04 16:35:44 -04:00
Vladimir Indic cb69616d46 PC sampling client: using raw pointers (#902)
* PC sampling client: using raw pointers to prevent premature destruction of buffers

* PCS client: freeing buffer_ids

[ROCm/rocprofiler-sdk commit: b0c41827c3]
2024-06-04 13:16:26 -05:00
Vladimir Indic b0c41827c3 PC sampling client: using raw pointers (#902)
* PC sampling client: using raw pointers to prevent premature destruction of buffers

* PCS client: freeing buffer_ids
2024-06-04 13:16:26 -05:00
Ammar ELWazir 1c0dcebe94 Update client.cpp (#900)
[ROCm/rocprofiler-sdk commit: 0e43a30de0]
2024-06-04 13:16:26 -05:00
Ammar ELWazir 0e43a30de0 Update client.cpp (#900) 2024-06-04 13:16:26 -05:00
Vladimir Indic 592d9edf6e PC sampling: CID manager unit test (#898)
[ROCm/rocprofiler-sdk commit: 1c5bf63dbc]
2024-06-04 13:16:26 -05:00
Vladimir Indic 1c5bf63dbc PC sampling: CID manager unit test (#898) 2024-06-04 13:16:26 -05:00
Ammar ELWazir 008c808174 DRM Issue Fix for SLES 15 (#897)
* DRM Issue Fix

* Formatting Fix

[ROCm/rocprofiler-sdk commit: 5347c124c5]
2024-06-04 13:16:26 -05:00
Ammar ELWazir 5347c124c5 DRM Issue Fix for SLES 15 (#897)
* DRM Issue Fix

* Formatting Fix
2024-06-04 13:16:26 -05:00
Galantsev, Dmitrii e11afbf60f Add GPU indexing and fix check for fields in rocprof
- Fix RUNPATH for tests

Change-Id: I79517592b49d27080a010a2e41e5878adf24a157
Signed-off-by: Galantsev, Dmitrii <dmitrii.galantsev@amd.com>
2024-06-04 12:56:22 -05:00
Galantsev, Dmitrii f73e123900 Add GPU indexing and fix check for fields in rocprof
- Fix RUNPATH for tests

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


[ROCm/rdc commit: e11afbf60f]
2024-06-04 12:56:22 -05:00
saurabhAMD 351a047627 Rotating tensor -R (default:off)
[ROCm/rccl-tests commit: 36a2c372ac]
2024-06-04 11:35:39 -05:00
saurabhAMD 36a2c372ac Rotating tensor -R (default:off) 2024-06-04 11:35:39 -05:00
Fabian Ritter 10b3a313d2 Add __device__ specifier to HIP's warpSize constexpr variable
The warpSize variable is set to the value of the __AMDGCN_WAVEFRONT_SIZE macro,
which is a meaningless default in host code.
The resolution for SWDEV-449015 will introduce diagnostics for uses of this
macro in host code, which includes the current definition of the warpSize
variable. With the __device__ specifier, the definition of the warpSize
variable will not cause these diagnostics.

This change does not stop the variable from being used in host code since clang
intentionally does not diagnose uses of __device__ constexpr variables in host
code.

Change-Id: I0317217affe94fdf2dfd9ad0f134e68f5173245f


[ROCm/clr commit: 819e537dc5]
2024-06-04 09:32:52 -04:00
Fabian Ritter 819e537dc5 Add __device__ specifier to HIP's warpSize constexpr variable
The warpSize variable is set to the value of the __AMDGCN_WAVEFRONT_SIZE macro,
which is a meaningless default in host code.
The resolution for SWDEV-449015 will introduce diagnostics for uses of this
macro in host code, which includes the current definition of the warpSize
variable. With the __device__ specifier, the definition of the warpSize
variable will not cause these diagnostics.

This change does not stop the variable from being used in host code since clang
intentionally does not diagnose uses of __device__ constexpr variables in host
code.

Change-Id: I0317217affe94fdf2dfd9ad0f134e68f5173245f
2024-06-04 09:32:52 -04:00