Skip to content

Tensilelite: Add BiasDataTypeList, support problem I8/I8/S, I8/I/S and misc bug fix - #14

Merged
aazz44ss merged 2 commits into
ROCm:developfrom
KKyang:multi_bias
Dec 7, 2022
Merged

Tensilelite: Add BiasDataTypeList, support problem I8/I8/S, I8/I/S and misc bug fix#14
aazz44ss merged 2 commits into
ROCm:developfrom
KKyang:multi_bias

Conversation

@KKyang

@KKyang KKyang commented Dec 5, 2022 •
edited
Loading

Copy link
Copy Markdown
Contributor

[Features]

  1. Add BiasDataTypeList, generates set(dataType, computeDataType, destDataType) by default if numRegisters() < 1
  2. Add BiasLDS and remove Bias global load
  3. Add I8/I8/S, I8/I/S (By Vin)

[Bugs]

  1. Fix glvw == 1 NN FP16 local write fail
  2. Fix glvw == 2 TN FP16 tail loop
  3. Set readToTmpVgpr=False for local write (By Vin)
  4. Let activation's temporary sgpr align 2 to avoid compiling error at s_setpc/swappc (By Vin)
  5. Fix activation bugin I32 (By Vin)

[Others]

  1. Add CSafeLoader
  2. Implement deepcopy for class Item
  3. Use fastdeepcopy in Activation.py
  4. Remove deepcopy in TensilePass

KKyang added 2 commits December 5, 2022 15:32
@KKyang
Remove magic number in ConstructRocblasltProblem
608395d 
Get max_workspace_bytes from pref
@KKyang
Tensilelite: Add BiasDataTypeList, support problem I8/I8/S, I8/I/S an…
d61f621 
…d misc bug fix

[Features]

1. Add BiasDataTypeList, generates
   set(dataType, computeDataType, destDataType) by default if
   numRegisters() < 1
2. Add BiasLDS and remove Bias global load
3. Add I8/I8/S, I8/I/S (By Vin)

[Bugs]

1. Fix glvw == 1 NN FP16 local write fail
2. Fix glvw == 2 TN FP16 tail loop
3. Set readToTmpVgpr=False for local write (By Vin)
4. Let activation's temporary sgpr align 2 to avoid compiling error
   at s_setpc/swappc (By Vin)
5. Fix activation bugin I32 (By Vin)

[Others]

1. Add CSafeLoader
2. Implement deepcopy for class Item
3. Use fastdeepcopy in Activation.py
4. Remove deepcopy in TensilePass
@jichangjichang jichangjichang mentioned this pull request Dec 6, 2022
Merged
@aazz44ss
aazz44ss merged commit befda4d into ROCm:develop Dec 7, 2022
@tsenwang tsenwang mentioned this pull request Aug 28, 2024
Merged
@tsenwang tsenwang mentioned this pull request Sep 18, 2024
Open
@tsenwang tsenwang mentioned this pull request Sep 25, 2024
Open
@tsenwang tsenwang mentioned this pull request Oct 29, 2024
Merged
yoichiyoshida pushed a commit that referenced this pull request Feb 27, 2025
@b-shi @msujon-AMD @adityalj
Add support of F8/F16/BF16 datatypes for Mi355 (#14)
36f3c32 
Incorporate new f8 design.
Add new f8,f16,bf16 kernel support for MI355
---------

Co-authored-by: Majed Sujon <mdmsujon@amd.com>
Co-authored-by: adijoshi <aditya.joshi@amd.com>
Co-authored-by: brian <brianshi@amd.com>
ryanswann-amd pushed a commit to ryanswann-amd/hipBLASLt that referenced this pull request Jun 19, 2025
@AlexBrownAMD
Merge pull request ROCm#14 from yenong-amd/OrigamiLibs
f50978b 
Add BBS custom 256x256x64 kernel with new logic
assistant-librarian Bot pushed a commit that referenced this pull request Nov 3, 2026
@rkayaith @assistant-librarian
[rocm-libraries] ROCm/rocm-libraries#14714 (commit d407b0f)
299438c 
fix(hipblaslt): release matmul descriptors on early exits
 (#14714)

JIRA ID : N/A

## Motivation

The test helper `testing_matmul_with_bias` destroys its matrix-layout
and matmul descriptors only at the end of the function. Any early return
leaks them, including the expected "NO solution found!" failure in
`rocroller_predicate_test.unrollXYK`. Found while expanding ASAN testing
in [#14240](ROCm/rocm-libraries#14240).

Current ASAN CI does not run this test. The expanded-coverage PR
[#14240](ROCm/rocm-libraries#14240) adds it to
scheduled standard ASAN runs on gfx950.

## Technical Details

Own each descriptor with a `std::unique_ptr` and its
`hipblasLtMatrixLayoutDestroy` or `hipblasLtMatmulDescDestroy` deleter
as soon as it is created, and remove the manual destruction at the end
of the function. The raw handle vectors remain because
`GroupedGemm::setProblem` takes vectors of raw handles.

## Test Plan

With a host AddressSanitizer (`HOST_ASAN`) client build on gfx950, run
from the repository root:

```sh
ASAN_OPTIONS=quarantine_size_mb=600:detect_leaks=1 \
LSAN_OPTIONS=suppressions=test/therock/lsan.supp \
hipblaslt-test --gtest_filter='*rocroller_predicate_test.unrollXYK*'
```

## Test Result

Leaked bytes went from 5,098 to 0.

<details>
<summary>ASAN error output (before fix)</summary>

```text
=================================================================
==377==ERROR: LeakSanitizer: detected memory leaks

Direct leak of 184 byte(s) in 1 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d895ba74 in rocblaslt_matmul_desc_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15ba74)
    #2 0x70f5d8becf3a in hipblasLtMatmulDescCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ecf3a)
    #3 0x63ceaafe903e in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda17'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #4 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #5 0x63ceaaf62403 in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e3403)
    #6 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #7 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #8 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

Direct leak of 56 byte(s) in 1 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d895ab5c in rocblaslt_matrix_layout_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15ab5c)
    #2 0x70f5d8bec5b2 in hipblasLtMatrixLayoutCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ec5b2)
    #3 0x63ceaafe626d in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda1'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #4 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #5 0x63ceaaf602e0 in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e12e0)
    #6 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #7 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #8 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

Direct leak of 56 byte(s) in 1 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d895ab5c in rocblaslt_matrix_layout_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15ab5c)
    #2 0x70f5d8bec5b2 in hipblasLtMatrixLayoutCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ec5b2)
    #3 0x63ceaafe665d in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda2'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #4 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #5 0x63ceaaf60546 in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e1546)
    #6 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #7 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #8 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

Direct leak of 56 byte(s) in 1 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d895ab5c in rocblaslt_matrix_layout_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15ab5c)
    #2 0x70f5d8bec5b2 in hipblasLtMatrixLayoutCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ec5b2)
    #3 0x63ceaafe5e7d in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda0'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #4 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #5 0x63ceaaf6007d in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e107d)
    #6 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #7 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #8 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

Direct leak of 56 byte(s) in 1 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d895ab5c in rocblaslt_matrix_layout_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15ab5c)
    #2 0x70f5d8bec5b2 in hipblasLtMatrixLayoutCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ec5b2)
    #3 0x63ceaafe5a8d in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #4 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #5 0x63ceaaf5fe0f in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e0e0f)
    #6 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #7 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #8 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

Indirect leak of 1976 byte(s) in 1 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d8a91976 in std::vector<TensileLite::TensorDescriptor, std::allocator<TensileLite::TensorDescriptor>>::vector(std::vector<TensileLite::TensorDescriptor, std::allocator<TensileLite::TensorDescriptor>> const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x291976)
    #2 0x70f5d8a916b8 in TensileLite::ContractionProblem::ContractionProblem(TensileLite::ContractionProblem const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x2916b8)
    #3 0x70f5d8a2b2ec in TensileLite::ContractionProblemGemm::ContractionProblemGemm(TensileLite::ContractionProblemGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x22b2ec)
    #4 0x70f5d8a93727 in TensileDataGemm::TensileDataGemm(TensileDataGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x293727)
    #5 0x70f5d89c045b in initTensileGemmData(_rocblaslt_handle*, rocblaslt::RocGemmType, hipblasOperation_t, hipblasOperation_t, hipDataType, hipDataType, hipDataType, hipDataType, rocblaslt_compute_type_, unsigned long, std::shared_ptr<void>&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x1c045b)
    #6 0x70f5d895bc78 in rocblaslt_matmul_desc_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15bc78)
    #7 0x70f5d8becf3a in hipblasLtMatmulDescCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ecf3a)
    #8 0x63ceaafe903e in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda17'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #9 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #10 0x63ceaaf62403 in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e3403)
    #11 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #12 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #13 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

Indirect leak of 1536 byte(s) in 1 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d89c03d2 in initTensileGemmData(_rocblaslt_handle*, rocblaslt::RocGemmType, hipblasOperation_t, hipblasOperation_t, hipDataType, hipDataType, hipDataType, hipDataType, rocblaslt_compute_type_, unsigned long, std::shared_ptr<void>&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x1c03d2)
    #2 0x70f5d895bc78 in rocblaslt_matmul_desc_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15bc78)
    #3 0x70f5d8becf3a in hipblasLtMatmulDescCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ecf3a)
    #4 0x63ceaafe903e in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda17'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #5 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #6 0x63ceaaf62403 in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e3403)
    #7 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #8 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #9 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

Indirect leak of 608 byte(s) in 1 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d8a91739 in TensileLite::ContractionProblem::ContractionProblem(TensileLite::ContractionProblem const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x291739)
    #2 0x70f5d8a2b2ec in TensileLite::ContractionProblemGemm::ContractionProblemGemm(TensileLite::ContractionProblemGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x22b2ec)
    #3 0x70f5d8a93727 in TensileDataGemm::TensileDataGemm(TensileDataGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x293727)
    #4 0x70f5d89c045b in initTensileGemmData(_rocblaslt_handle*, rocblaslt::RocGemmType, hipblasOperation_t, hipblasOperation_t, hipDataType, hipDataType, hipDataType, hipDataType, rocblaslt_compute_type_, unsigned long, std::shared_ptr<void>&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x1c045b)
    #5 0x70f5d895bc78 in rocblaslt_matmul_desc_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15bc78)
    #6 0x70f5d8becf3a in hipblasLtMatmulDescCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ecf3a)
    #7 0x63ceaafe903e in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda17'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #8 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #9 0x63ceaaf62403 in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e3403)
    #10 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #11 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #12 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

Indirect leak of 96 byte(s) in 4 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d8a91dd9 in TensileLite::TensorDescriptor::TensorDescriptor(TensileLite::TensorDescriptor const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x291dd9)
    #2 0x70f5d8a91a2a in std::vector<TensileLite::TensorDescriptor, std::allocator<TensileLite::TensorDescriptor>>::vector(std::vector<TensileLite::TensorDescriptor, std::allocator<TensileLite::TensorDescriptor>> const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x291a2a)
    #3 0x70f5d8a916b8 in TensileLite::ContractionProblem::ContractionProblem(TensileLite::ContractionProblem const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x2916b8)
    #4 0x70f5d8a2b2ec in TensileLite::ContractionProblemGemm::ContractionProblemGemm(TensileLite::ContractionProblemGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x22b2ec)
    #5 0x70f5d8a93727 in TensileDataGemm::TensileDataGemm(TensileDataGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x293727)
    #6 0x70f5d89c045b in initTensileGemmData(_rocblaslt_handle*, rocblaslt::RocGemmType, hipblasOperation_t, hipblasOperation_t, hipDataType, hipDataType, hipDataType, hipDataType, rocblaslt_compute_type_, unsigned long, std::shared_ptr<void>&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x1c045b)
    #7 0x70f5d895bc78 in rocblaslt_matmul_desc_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15bc78)
    #8 0x70f5d8becf3a in hipblasLtMatmulDescCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ecf3a)
    #9 0x63ceaafe903e in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda17'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #10 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #11 0x63ceaaf62403 in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e3403)
    #12 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #13 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #14 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

Indirect leak of 96 byte(s) in 4 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d8a91f25 in TensileLite::TensorDescriptor::TensorDescriptor(TensileLite::TensorDescriptor const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x291f25)
    #2 0x70f5d8a91a2a in std::vector<TensileLite::TensorDescriptor, std::allocator<TensileLite::TensorDescriptor>>::vector(std::vector<TensileLite::TensorDescriptor, std::allocator<TensileLite::TensorDescriptor>> const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x291a2a)
    #3 0x70f5d8a916b8 in TensileLite::ContractionProblem::ContractionProblem(TensileLite::ContractionProblem const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x2916b8)
    #4 0x70f5d8a2b2ec in TensileLite::ContractionProblemGemm::ContractionProblemGemm(TensileLite::ContractionProblemGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x22b2ec)
    #5 0x70f5d8a93727 in TensileDataGemm::TensileDataGemm(TensileDataGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x293727)
    #6 0x70f5d89c045b in initTensileGemmData(_rocblaslt_handle*, rocblaslt::RocGemmType, hipblasOperation_t, hipblasOperation_t, hipDataType, hipDataType, hipDataType, hipDataType, rocblaslt_compute_type_, unsigned long, std::shared_ptr<void>&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x1c045b)
    #7 0x70f5d895bc78 in rocblaslt_matmul_desc_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15bc78)
    #8 0x70f5d8becf3a in hipblasLtMatmulDescCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ecf3a)
    #9 0x63ceaafe903e in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda17'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #10 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #11 0x63ceaaf62403 in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e3403)
    #12 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #13 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #14 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

Indirect leak of 96 byte(s) in 1 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d8a2d783 in TensileLite::ContractionProblemGemm::ContractionProblemGemm(TensileLite::ContractionProblemGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x22d783)
    #2 0x70f5d8a93727 in TensileDataGemm::TensileDataGemm(TensileDataGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x293727)
    #3 0x70f5d89c045b in initTensileGemmData(_rocblaslt_handle*, rocblaslt::RocGemmType, hipblasOperation_t, hipblasOperation_t, hipDataType, hipDataType, hipDataType, hipDataType, rocblaslt_compute_type_, unsigned long, std::shared_ptr<void>&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x1c045b)
    #4 0x70f5d895bc78 in rocblaslt_matmul_desc_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15bc78)
    #5 0x70f5d8becf3a in hipblasLtMatmulDescCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ecf3a)
    #6 0x63ceaafe903e in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda17'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #7 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #8 0x63ceaaf62403 in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e3403)
    #9 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #10 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #11 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

Indirect leak of 64 byte(s) in 1 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d8a2cbd5 in TensileLite::ContractionProblemGemm::ContractionProblemGemm(TensileLite::ContractionProblemGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x22cbd5)
    #2 0x70f5d8a93727 in TensileDataGemm::TensileDataGemm(TensileDataGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x293727)
    #3 0x70f5d89c045b in initTensileGemmData(_rocblaslt_handle*, rocblaslt::RocGemmType, hipblasOperation_t, hipblasOperation_t, hipDataType, hipDataType, hipDataType, hipDataType, rocblaslt_compute_type_, unsigned long, std::shared_ptr<void>&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x1c045b)
    #4 0x70f5d895bc78 in rocblaslt_matmul_desc_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15bc78)
    #5 0x70f5d8becf3a in hipblasLtMatmulDescCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ecf3a)
    #6 0x63ceaafe903e in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda17'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #7 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #8 0x63ceaaf62403 in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e3403)
    #9 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #10 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #11 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

Indirect leak of 34 byte(s) in 1 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d8a2c56e in TensileLite::ContractionProblemGemm::ContractionProblemGemm(TensileLite::ContractionProblemGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x22c56e)
    #2 0x70f5d8a93727 in TensileDataGemm::TensileDataGemm(TensileDataGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x293727)
    #3 0x70f5d89c045b in initTensileGemmData(_rocblaslt_handle*, rocblaslt::RocGemmType, hipblasOperation_t, hipblasOperation_t, hipDataType, hipDataType, hipDataType, hipDataType, rocblaslt_compute_type_, unsigned long, std::shared_ptr<void>&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x1c045b)
    #4 0x70f5d895bc78 in rocblaslt_matmul_desc_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15bc78)
    #5 0x70f5d8becf3a in hipblasLtMatmulDescCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ecf3a)
    #6 0x63ceaafe903e in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda17'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #7 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #8 0x63ceaaf62403 in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e3403)
    #9 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #10 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #11 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

Indirect leak of 32 byte(s) in 1 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d8a2ca60 in TensileLite::ContractionProblemGemm::ContractionProblemGemm(TensileLite::ContractionProblemGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x22ca60)
    #2 0x70f5d8a93727 in TensileDataGemm::TensileDataGemm(TensileDataGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x293727)
    #3 0x70f5d89c045b in initTensileGemmData(_rocblaslt_handle*, rocblaslt::RocGemmType, hipblasOperation_t, hipblasOperation_t, hipDataType, hipDataType, hipDataType, hipDataType, rocblaslt_compute_type_, unsigned long, std::shared_ptr<void>&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x1c045b)
    #4 0x70f5d895bc78 in rocblaslt_matmul_desc_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15bc78)
    #5 0x70f5d8becf3a in hipblasLtMatmulDescCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ecf3a)
    #6 0x63ceaafe903e in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda17'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #7 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #8 0x63ceaaf62403 in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e3403)
    #9 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #10 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #11 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

Indirect leak of 32 byte(s) in 1 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d8a2d607 in TensileLite::ContractionProblemGemm::ContractionProblemGemm(TensileLite::ContractionProblemGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x22d607)
    #2 0x70f5d8a93727 in TensileDataGemm::TensileDataGemm(TensileDataGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x293727)
    #3 0x70f5d89c045b in initTensileGemmData(_rocblaslt_handle*, rocblaslt::RocGemmType, hipblasOperation_t, hipblasOperation_t, hipDataType, hipDataType, hipDataType, hipDataType, rocblaslt_compute_type_, unsigned long, std::shared_ptr<void>&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x1c045b)
    #4 0x70f5d895bc78 in rocblaslt_matmul_desc_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15bc78)
    #5 0x70f5d8becf3a in hipblasLtMatmulDescCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ecf3a)
    #6 0x63ceaafe903e in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda17'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #7 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #8 0x63ceaaf62403 in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e3403)
    #9 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #10 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #11 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

Indirect leak of 32 byte(s) in 1 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d8a2cd47 in TensileLite::ContractionProblemGemm::ContractionProblemGemm(TensileLite::ContractionProblemGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x22cd47)
    #2 0x70f5d8a93727 in TensileDataGemm::TensileDataGemm(TensileDataGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x293727)
    #3 0x70f5d89c045b in initTensileGemmData(_rocblaslt_handle*, rocblaslt::RocGemmType, hipblasOperation_t, hipblasOperation_t, hipDataType, hipDataType, hipDataType, hipDataType, rocblaslt_compute_type_, unsigned long, std::shared_ptr<void>&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x1c045b)
    #4 0x70f5d895bc78 in rocblaslt_matmul_desc_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15bc78)
    #5 0x70f5d8becf3a in hipblasLtMatmulDescCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ecf3a)
    #6 0x63ceaafe903e in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda17'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #7 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #8 0x63ceaaf62403 in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e3403)
    #9 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #10 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #11 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

Indirect leak of 32 byte(s) in 1 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d8a2c8e5 in TensileLite::ContractionProblemGemm::ContractionProblemGemm(TensileLite::ContractionProblemGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x22c8e5)
    #2 0x70f5d8a93727 in TensileDataGemm::TensileDataGemm(TensileDataGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x293727)
    #3 0x70f5d89c045b in initTensileGemmData(_rocblaslt_handle*, rocblaslt::RocGemmType, hipblasOperation_t, hipblasOperation_t, hipDataType, hipDataType, hipDataType, hipDataType, rocblaslt_compute_type_, unsigned long, std::shared_ptr<void>&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x1c045b)
    #4 0x70f5d895bc78 in rocblaslt_matmul_desc_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15bc78)
    #5 0x70f5d8becf3a in hipblasLtMatmulDescCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ecf3a)
    #6 0x63ceaafe903e in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda17'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #7 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #8 0x63ceaaf62403 in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e3403)
    #9 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #10 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #11 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

Indirect leak of 24 byte(s) in 1 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d8a2ceca in TensileLite::ContractionProblemGemm::ContractionProblemGemm(TensileLite::ContractionProblemGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x22ceca)
    #2 0x70f5d8a93727 in TensileDataGemm::TensileDataGemm(TensileDataGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x293727)
    #3 0x70f5d89c045b in initTensileGemmData(_rocblaslt_handle*, rocblaslt::RocGemmType, hipblasOperation_t, hipblasOperation_t, hipDataType, hipDataType, hipDataType, hipDataType, rocblaslt_compute_type_, unsigned long, std::shared_ptr<void>&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x1c045b)
    #4 0x70f5d895bc78 in rocblaslt_matmul_desc_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15bc78)
    #5 0x70f5d8becf3a in hipblasLtMatmulDescCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ecf3a)
    #6 0x63ceaafe903e in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda17'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #7 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #8 0x63ceaaf62403 in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e3403)
    #9 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #10 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #11 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

Indirect leak of 8 byte(s) in 1 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d8a2d1ae in TensileLite::ContractionProblemGemm::ContractionProblemGemm(TensileLite::ContractionProblemGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x22d1ae)
    #2 0x70f5d8a93727 in TensileDataGemm::TensileDataGemm(TensileDataGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x293727)
    #3 0x70f5d89c045b in initTensileGemmData(_rocblaslt_handle*, rocblaslt::RocGemmType, hipblasOperation_t, hipblasOperation_t, hipDataType, hipDataType, hipDataType, hipDataType, rocblaslt_compute_type_, unsigned long, std::shared_ptr<void>&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x1c045b)
    #4 0x70f5d895bc78 in rocblaslt_matmul_desc_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15bc78)
    #5 0x70f5d8becf3a in hipblasLtMatmulDescCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ecf3a)
    #6 0x63ceaafe903e in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda17'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #7 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #8 0x63ceaaf62403 in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e3403)
    #9 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #10 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #11 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

Indirect leak of 8 byte(s) in 1 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d8a2d31c in TensileLite::ContractionProblemGemm::ContractionProblemGemm(TensileLite::ContractionProblemGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x22d31c)
    #2 0x70f5d8a93727 in TensileDataGemm::TensileDataGemm(TensileDataGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x293727)
    #3 0x70f5d89c045b in initTensileGemmData(_rocblaslt_handle*, rocblaslt::RocGemmType, hipblasOperation_t, hipblasOperation_t, hipDataType, hipDataType, hipDataType, hipDataType, rocblaslt_compute_type_, unsigned long, std::shared_ptr<void>&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x1c045b)
    #4 0x70f5d895bc78 in rocblaslt_matmul_desc_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15bc78)
    #5 0x70f5d8becf3a in hipblasLtMatmulDescCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ecf3a)
    #6 0x63ceaafe903e in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda17'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #7 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #8 0x63ceaaf62403 in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e3403)
    #9 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #10 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #11 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

Indirect leak of 8 byte(s) in 1 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d8a2d040 in TensileLite::ContractionProblemGemm::ContractionProblemGemm(TensileLite::ContractionProblemGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x22d040)
    #2 0x70f5d8a93727 in TensileDataGemm::TensileDataGemm(TensileDataGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x293727)
    #3 0x70f5d89c045b in initTensileGemmData(_rocblaslt_handle*, rocblaslt::RocGemmType, hipblasOperation_t, hipblasOperation_t, hipDataType, hipDataType, hipDataType, hipDataType, rocblaslt_compute_type_, unsigned long, std::shared_ptr<void>&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x1c045b)
    #4 0x70f5d895bc78 in rocblaslt_matmul_desc_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15bc78)
    #5 0x70f5d8becf3a in hipblasLtMatmulDescCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ecf3a)
    #6 0x63ceaafe903e in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda17'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #7 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #8 0x63ceaaf62403 in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e3403)
    #9 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #10 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #11 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

Indirect leak of 8 byte(s) in 1 object(s) allocated from:
    #0 0x70f5d9d6d8cd in operator new(unsigned long) /__w/rocm-libraries/rocm-libraries/TheRock/compiler/amd-llvm/compiler-rt/lib/asan/asan_new_delete.cpp:109:35
    #1 0x70f5d8a2d48d in TensileLite::ContractionProblemGemm::ContractionProblemGemm(TensileLite::ContractionProblemGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x22d48d)
    #2 0x70f5d8a93727 in TensileDataGemm::TensileDataGemm(TensileDataGemm const&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x293727)
    #3 0x70f5d89c045b in initTensileGemmData(_rocblaslt_handle*, rocblaslt::RocGemmType, hipblasOperation_t, hipblasOperation_t, hipDataType, hipDataType, hipDataType, hipDataType, rocblaslt_compute_type_, unsigned long, std::shared_ptr<void>&) (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x1c045b)
    #4 0x70f5d895bc78 in rocblaslt_matmul_desc_create (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x15bc78)
    #5 0x70f5d8becf3a in hipblasLtMatmulDescCreate (/__w/rocm-libraries/rocm-libraries/build/lib/libhipblaslt.so.1+0x3ecf3a)
    #6 0x63ceaafe903e in std::_Function_handler<void (), testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType)::'lambda17'()>::_M_invoke(std::_Any_data const&) matmul_gtest.cpp
    #7 0x63ceaae5e765 in catch_signals_and_exceptions_as_failures(std::function<void ()>, bool) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x4df765)
    #8 0x63ceaaf62403 in testing_matmul_with_bias(Arguments const&, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType, hipDataType) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5e3403)
    #9 0x63ceaaf501b8 in testing_matmul(Arguments const&) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x5d11b8)
    #10 0x63ceab034c8f in (anonymous namespace)::rocroller_predicate_test_unrollXYK_Test::TestBody() matmul_gtest.cpp
    #11 0x63ceaba7023c in void testing::internal::HandleExceptionsInMethodIfSupported<testing::Test, void>(testing::Test*, void (testing::Test::*)(), char const*) (/__w/rocm-libraries/rocm-libraries/build/bin/hipblaslt-test+0x10f123c)

SUMMARY: AddressSanitizer: 5098 byte(s) leaked in 28 allocation(s).
```

</details>

## Submission Checklist

- [ ] Look over the contributing guidelines at
https://github.com/ROCm/TheRock/blob/main/GOVERNANCE.md#pull-requests.

## Risk level

Low (2/5): changes test-client descriptor ownership;
matrix-multiplication library behavior is unchanged.
Sign up for free to join this conversation on GitHub. Already have an account? Sign in to comment

Reviewers

@jichangjichang jichangjichang Awaiting requested review from jichangjichang jichangjichang is a code owner
1 more reviewer
@aazz44ss aazz44ss aazz44ss approved these changes
Reviewers whose approvals may not affect merge requirements

Assignees

No one assigned

Labels

None yet

Projects

None yet

Milestone

No milestone

Development

Successfully merging this pull request may close these issues.

2 participants

@KKyang @aazz44ss