From 73f3adf0bdd2eae54fbcc74c8fbcbf1ea1d0accd Mon Sep 17 00:00:00 2001 From: tarafdarTT Date: Thu, 4 Jul 2024 19:35:43 +0000 Subject: [PATCH] #9744: migrate kernels --- .../op_library/unpad/multi_core/unpad_op_multi_core.cpp | 6 +++--- .../reader_unary_unpad_dims_interleaved_start_id.cpp | 0 .../reader_unary_unpad_dims_rm_interleaved_start_id.cpp | 0 .../writer_unary_stick_layout_interleaved_start_id.cpp | 0 4 files changed, 3 insertions(+), 3 deletions(-) rename ttnn/cpp/ttnn/operations/data_movement/slice/{ => device}/kernels/dataflow/reader_unary_unpad_dims_interleaved_start_id.cpp (100%) rename ttnn/cpp/ttnn/operations/data_movement/slice/{ => device}/kernels/dataflow/reader_unary_unpad_dims_rm_interleaved_start_id.cpp (100%) rename ttnn/cpp/ttnn/operations/data_movement/slice/{ => device}/kernels/dataflow/writer_unary_stick_layout_interleaved_start_id.cpp (100%) diff --git a/tt_eager/tt_dnn/op_library/unpad/multi_core/unpad_op_multi_core.cpp b/tt_eager/tt_dnn/op_library/unpad/multi_core/unpad_op_multi_core.cpp index a5427189e02..fd1bbbd8b60 100644 --- a/tt_eager/tt_dnn/op_library/unpad/multi_core/unpad_op_multi_core.cpp +++ b/tt_eager/tt_dnn/op_library/unpad/multi_core/unpad_op_multi_core.cpp @@ -161,13 +161,13 @@ operation::ProgramWithCallbacks unpad_rm_multi_core( tt_metal::KernelHandle unary_reader_kernel_id = tt_metal::CreateKernel( program, - "ttnn/cpp/ttnn/operations/data_movement/slice/kernels/dataflow/reader_unary_unpad_dims_rm_interleaved_start_id.cpp", + "ttnn/cpp/ttnn/operations/data_movement/slice/device/kernels/dataflow/reader_unary_unpad_dims_rm_interleaved_start_id.cpp", total_cores, tt_metal::ReaderDataMovementConfig(reader_compile_time_args_vec)); tt_metal::KernelHandle unary_writer_kernel_id = tt_metal::CreateKernel( program, - "ttnn/cpp/ttnn/operations/data_movement/slice/kernels/dataflow/writer_unary_stick_layout_interleaved_start_id.cpp", + "ttnn/cpp/ttnn/operations/data_movement/slice/device/kernels/dataflow/writer_unary_stick_layout_interleaved_start_id.cpp", total_cores, tt_metal::WriterDataMovementConfig(writer_compile_time_args_vec)); @@ -435,7 +435,7 @@ operation::ProgramWithCallbacks unpad_tile_multi_core( // Tilized reader tt_metal::KernelHandle unary_reader_kernel_id = tt_metal::CreateKernel( program, - "ttnn/cpp/ttnn/operations/data_movement/slice/kernels/dataflow/reader_unary_unpad_dims_interleaved_start_id.cpp", + "ttnn/cpp/ttnn/operations/data_movement/slice/device/kernels/dataflow/reader_unary_unpad_dims_interleaved_start_id.cpp", total_cores, tt_metal::ReaderDataMovementConfig(reader_compile_time_args)); diff --git a/ttnn/cpp/ttnn/operations/data_movement/slice/kernels/dataflow/reader_unary_unpad_dims_interleaved_start_id.cpp b/ttnn/cpp/ttnn/operations/data_movement/slice/device/kernels/dataflow/reader_unary_unpad_dims_interleaved_start_id.cpp similarity index 100% rename from ttnn/cpp/ttnn/operations/data_movement/slice/kernels/dataflow/reader_unary_unpad_dims_interleaved_start_id.cpp rename to ttnn/cpp/ttnn/operations/data_movement/slice/device/kernels/dataflow/reader_unary_unpad_dims_interleaved_start_id.cpp diff --git a/ttnn/cpp/ttnn/operations/data_movement/slice/kernels/dataflow/reader_unary_unpad_dims_rm_interleaved_start_id.cpp b/ttnn/cpp/ttnn/operations/data_movement/slice/device/kernels/dataflow/reader_unary_unpad_dims_rm_interleaved_start_id.cpp similarity index 100% rename from ttnn/cpp/ttnn/operations/data_movement/slice/kernels/dataflow/reader_unary_unpad_dims_rm_interleaved_start_id.cpp rename to ttnn/cpp/ttnn/operations/data_movement/slice/device/kernels/dataflow/reader_unary_unpad_dims_rm_interleaved_start_id.cpp diff --git a/ttnn/cpp/ttnn/operations/data_movement/slice/kernels/dataflow/writer_unary_stick_layout_interleaved_start_id.cpp b/ttnn/cpp/ttnn/operations/data_movement/slice/device/kernels/dataflow/writer_unary_stick_layout_interleaved_start_id.cpp similarity index 100% rename from ttnn/cpp/ttnn/operations/data_movement/slice/kernels/dataflow/writer_unary_stick_layout_interleaved_start_id.cpp rename to ttnn/cpp/ttnn/operations/data_movement/slice/device/kernels/dataflow/writer_unary_stick_layout_interleaved_start_id.cpp