From b1f3b08419be073b210b99cc3c755e464df1ca97 Mon Sep 17 00:00:00 2001 From: Anil Mahmud Date: Wed, 9 Oct 2024 16:42:14 -0400 Subject: [PATCH] #13548: Remove default argument values for DstSync parameter --- .../blackhole/metal/llk_api/llk_math_unary_datacopy_api.h | 4 ++-- .../grayskull/metal/llk_api/llk_math_unary_datacopy_api.h | 2 +- tt_metal/hw/ckernels/grayskull/metal/llk_api/llk_pack_api.h | 4 ++-- .../wormhole_b0/metal/llk_api/llk_math_unary_datacopy_api.h | 4 ++-- tt_metal/third_party/tt_llk_blackhole | 2 +- tt_metal/third_party/tt_llk_grayskull | 2 +- tt_metal/third_party/tt_llk_wormhole_b0 | 2 +- 7 files changed, 10 insertions(+), 10 deletions(-) diff --git a/tt_metal/hw/ckernels/blackhole/metal/llk_api/llk_math_unary_datacopy_api.h b/tt_metal/hw/ckernels/blackhole/metal/llk_api/llk_math_unary_datacopy_api.h index d8615fb6889..d0774799637 100644 --- a/tt_metal/hw/ckernels/blackhole/metal/llk_api/llk_math_unary_datacopy_api.h +++ b/tt_metal/hw/ckernels/blackhole/metal/llk_api/llk_math_unary_datacopy_api.h @@ -18,7 +18,7 @@ template < bool unpack_to_dest = false> inline void llk_math_eltwise_unary_datacopy(uint dst_index, uint operand = 0) { const std::uint32_t operand_id = get_operand_id(operand); - _llk_math_eltwise_unary_datacopy_( + _llk_math_eltwise_unary_datacopy_( dst_index, unpack_src_format[operand_id], unpack_dst_format[operand_id]); } @@ -33,8 +33,8 @@ inline void llk_math_eltwise_unary_datacopy_block(uint start_dst_index, uint nti for (uint32_t dst_index = start_dst_index; dst_index < start_dst_index + ntiles; dst_index++) { _llk_math_eltwise_unary_datacopy_< type, - src_b_bcast_type, DST_SYNC_MODE, + src_b_bcast_type, is_fp32_dest_acc_en, unpack_to_dest>(dst_index, unpack_src_format[operand_id], unpack_dst_format[operand_id]); } diff --git a/tt_metal/hw/ckernels/grayskull/metal/llk_api/llk_math_unary_datacopy_api.h b/tt_metal/hw/ckernels/grayskull/metal/llk_api/llk_math_unary_datacopy_api.h index 7f8e90e54dc..0441eda7503 100644 --- a/tt_metal/hw/ckernels/grayskull/metal/llk_api/llk_math_unary_datacopy_api.h +++ b/tt_metal/hw/ckernels/grayskull/metal/llk_api/llk_math_unary_datacopy_api.h @@ -17,7 +17,7 @@ template < bool unpack_to_dest = false> inline void llk_math_eltwise_unary_datacopy(uint dst_index, uint operand = 0 /* unused */) { - _llk_math_eltwise_unary_datacopy_(dst_index); + _llk_math_eltwise_unary_datacopy_(dst_index); } template diff --git a/tt_metal/hw/ckernels/grayskull/metal/llk_api/llk_pack_api.h b/tt_metal/hw/ckernels/grayskull/metal/llk_api/llk_pack_api.h index 9960adf52e7..cd6fc417659 100644 --- a/tt_metal/hw/ckernels/grayskull/metal/llk_api/llk_pack_api.h +++ b/tt_metal/hw/ckernels/grayskull/metal/llk_api/llk_pack_api.h @@ -113,7 +113,7 @@ inline void llk_pack(std::uint32_t tile_index, std::uint32_t output, std::uint32 std::uint32_t pack_tile_addr = get_output_tile_address(output_id, output_tile_index); - _llk_pack_( + _llk_pack_( tile_index, pack_dst_format[output_id], pack_tile_addr @@ -282,7 +282,7 @@ inline void llk_matmul_pack(const std::uint32_t start_tile_index, const std::uin std::uint32_t pack_tile_addr = get_output_tile_address(output_id, output_tile_index); - _llk_pack_( + _llk_pack_( tile_index, pack_dst_format[output_id], pack_tile_addr diff --git a/tt_metal/hw/ckernels/wormhole_b0/metal/llk_api/llk_math_unary_datacopy_api.h b/tt_metal/hw/ckernels/wormhole_b0/metal/llk_api/llk_math_unary_datacopy_api.h index 4b980b31d5b..0d8fa0e9f87 100644 --- a/tt_metal/hw/ckernels/wormhole_b0/metal/llk_api/llk_math_unary_datacopy_api.h +++ b/tt_metal/hw/ckernels/wormhole_b0/metal/llk_api/llk_math_unary_datacopy_api.h @@ -18,7 +18,7 @@ template < bool unpack_to_dest = false> inline void llk_math_eltwise_unary_datacopy(uint dst_index, uint operand = 0) { const std::uint32_t operand_id = get_operand_id(operand); - _llk_math_eltwise_unary_datacopy_( + _llk_math_eltwise_unary_datacopy_( dst_index, unpack_src_format[operand_id], unpack_dst_format[operand_id]); } @@ -31,7 +31,7 @@ inline void llk_math_eltwise_unary_datacopy_block(uint start_dst_index, uint nti const std::uint32_t operand_id = get_operand_id(operand); for (uint32_t dst_index = start_dst_index; dst_index < start_dst_index + ntiles; dst_index++) { - _llk_math_eltwise_unary_datacopy_( + _llk_math_eltwise_unary_datacopy_( dst_index, unpack_src_format[operand_id], unpack_dst_format[operand_id]); } } diff --git a/tt_metal/third_party/tt_llk_blackhole b/tt_metal/third_party/tt_llk_blackhole index ea1149109d9..3a9f90995fd 160000 --- a/tt_metal/third_party/tt_llk_blackhole +++ b/tt_metal/third_party/tt_llk_blackhole @@ -1 +1 @@ -Subproject commit ea1149109d9a530290936790c6620f9f99263f4e +Subproject commit 3a9f90995fd7bc0489145092ba0bd165543332a5 diff --git a/tt_metal/third_party/tt_llk_grayskull b/tt_metal/third_party/tt_llk_grayskull index eda31ada422..9cadb14bc90 160000 --- a/tt_metal/third_party/tt_llk_grayskull +++ b/tt_metal/third_party/tt_llk_grayskull @@ -1 +1 @@ -Subproject commit eda31ada422e8a7999d46823aa476e3487397093 +Subproject commit 9cadb14bc905b84abb0e99e41ab83a612c4cd428 diff --git a/tt_metal/third_party/tt_llk_wormhole_b0 b/tt_metal/third_party/tt_llk_wormhole_b0 index bbe1d58b375..7592e7b802d 160000 --- a/tt_metal/third_party/tt_llk_wormhole_b0 +++ b/tt_metal/third_party/tt_llk_wormhole_b0 @@ -1 +1 @@ -Subproject commit bbe1d58b37506cd5bbf9786734059725dd94df88 +Subproject commit 7592e7b802d99f142ee267e82dee84971ef7ee18