Skip to content

Commit

Permalink
#2749: Copy all metal kernels into metal test kernels
Browse files Browse the repository at this point in the history
  • Loading branch information
@DrJessop @tt-rkim
DrJessop authored and tt-rkim committed Oct 25, 2023
1 parent ea63ecb commit 0a8950e
Show file tree
Hide file tree
Showing 187 changed files with 9,174 additions and 245 deletions.
6 changes: 3 additions & 3 deletions tests/tt_metal/tt_metal/test_3x3conv_as_matmul_large_block.cpp
View file
Original file line number Diff line number Diff line change
Expand Up @@ -200,7 +200,7 @@ int main(int argc, char **argv) {

auto generic_binary_reader_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/generic_binary_reader_blocked.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/generic_binary_reader_blocked.cpp",
core,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_1, .noc = tt_metal::NOC::RISCV_1_default});

Expand All @@ -218,7 +218,7 @@ int main(int argc, char **argv) {

auto unary_writer_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/writer_unswizzle.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/writer_unswizzle.cpp",
core,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_0, .noc = tt_metal::NOC::RISCV_0_default});

Expand Down Expand Up @@ -251,7 +251,7 @@ int main(int argc, char **argv) {

auto mm_kernel = tt_metal::CreateComputeKernel(
program,
"tt_metal/kernels/compute/matmul_large_block_zm.cpp",
"tests/tt_metal/tt_metal/test_kernels/compute/matmul_large_block_zm.cpp",
core,
tt_metal::ComputeConfig{.compile_args = compute_kernel_args}
);
Expand Down
2 changes: 1 addition & 1 deletion tests/tt_metal/tt_metal/test_add_two_ints.cpp
View file
Original file line number Diff line number Diff line change
Expand Up @@ -40,7 +40,7 @@ int main(int argc, char **argv) {
std::vector<uint32_t> second_runtime_args = {303, 606};

tt_metal::KernelID add_two_ints_kernel = tt_metal::CreateDataMovementKernel(
program, "tt_metal/kernels/riscv_draft/add_two_ints.cpp", core,
program, "tests/tt_metal/tt_metal/test_kernels/misc/add_two_ints.cpp", core,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_0, .noc = tt_metal::NOC::RISCV_0_default});

////////////////////////////////////////////////////////////////////////////
Expand Down
22 changes: 11 additions & 11 deletions tests/tt_metal/tt_metal/test_bcast.cpp
View file
Original file line number Diff line number Diff line change
Expand Up @@ -28,26 +28,26 @@ const char* get_reader_name(bool multibank, BcastDim::Enum bcast_dim) {
TT_ASSERT(multibank && "Only multibank is supported correctly.");
if (bcast_dim == BcastDim::H) {
return multibank ?
"tt_metal/kernels/dataflow/reader_bcast_h_8bank.cpp" :
"tt_metal/kernels/dataflow/reader_bcast_h.cpp";
"tests/tt_metal/tt_metal/test_kernels/dataflow/reader_bcast_h_8bank.cpp" :
"tests/tt_metal/tt_metal/test_kernels/dataflow/reader_bcast_h.cpp";
} else if (bcast_dim == BcastDim::W) {
return multibank ?
"tt_metal/kernels/dataflow/reader_bcast_w_8bank.cpp" :
"tt_metal/kernels/dataflow/reader_bcast_w.cpp";
"tests/tt_metal/tt_metal/test_kernels/dataflow/reader_bcast_w_8bank.cpp" :
"tests/tt_metal/tt_metal/test_kernels/dataflow/reader_bcast_w.cpp";
} if (bcast_dim == BcastDim::HW) {
return multibank ?
"tt_metal/kernels/dataflow/reader_bcast_hw_8bank.cpp" :
"tt_metal/kernels/dataflow/reader_binary_diff_lengths.cpp";
"tests/tt_metal/tt_metal/test_kernels/dataflow/reader_bcast_hw_8bank.cpp" :
"tests/tt_metal/tt_metal/test_kernels/dataflow/reader_binary_diff_lengths.cpp";
}
TT_ASSERT(false && "Unexpected bcast_dim!");
return "";
}

const char* get_compute_name(BcastDim::Enum bcast_dim) {
switch (bcast_dim) {
case BcastDim::H: return "tt_metal/kernels/compute/bcast_h.cpp";
case BcastDim::W: return "tt_metal/kernels/compute/bcast_w.cpp";
case BcastDim::HW: return "tt_metal/kernels/compute/bcast_hw.cpp";
case BcastDim::H: return "tests/tt_metal/tt_metal/test_kernels/compute/bcast_h.cpp";
case BcastDim::W: return "tests/tt_metal/tt_metal/test_kernels/compute/bcast_w.cpp";
case BcastDim::HW: return "tests/tt_metal/tt_metal/test_kernels/compute/bcast_hw.cpp";
default: TT_ASSERT(false && "Unexpected bcast_dim!");
}
return "";
Expand Down Expand Up @@ -214,8 +214,8 @@ int main(int argc, char **argv) {

auto unary_writer_kernel = tt_metal::CreateDataMovementKernel(
program,
multibank ? "tt_metal/kernels/dataflow/writer_unary_8bank.cpp"
: "tt_metal/kernels/dataflow/writer_unary.cpp",
multibank ? "tests/tt_metal/tt_metal/test_kernels/dataflow/writer_unary_8bank.cpp"
: "tests/tt_metal/tt_metal/test_kernels/dataflow/writer_unary.cpp",
core,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_0, .noc = tt_metal::NOC::RISCV_0_default});

Expand Down
6 changes: 3 additions & 3 deletions tests/tt_metal/tt_metal/test_bmm.cpp
View file
Original file line number Diff line number Diff line change
Expand Up @@ -77,13 +77,13 @@ int main(int argc, char **argv) {
std::vector<uint32_t> writer_compile_time_args = {(uint32_t)dst_is_dram};
auto reader = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/reader_bmm_8bank.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/reader_bmm_8bank.cpp",
core,
DataMovementConfig{.processor = DataMovementProcessor::RISCV_1, .noc = NOC::RISCV_1_default, .compile_args = reader_compile_time_args});

auto writer = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/writer_bmm_8bank.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/writer_bmm_8bank.cpp",
core,
DataMovementConfig{.processor = DataMovementProcessor::RISCV_0, .noc = NOC::RISCV_0_default, .compile_args = writer_compile_time_args});

Expand All @@ -96,7 +96,7 @@ int main(int argc, char **argv) {

auto eltwise_binary_kernel = tt_metal::CreateComputeKernel(
program,
"tt_metal/kernels/compute/bmm.cpp",
"tests/tt_metal/tt_metal/test_kernels/compute/bmm.cpp",
core,
tt_metal::ComputeConfig{.compile_args = compute_kernel_args}
);
Expand Down
6 changes: 3 additions & 3 deletions tests/tt_metal/tt_metal/test_compile_args.cpp
View file
Original file line number Diff line number Diff line change
Expand Up @@ -35,13 +35,13 @@ bool test_compile_args(std::vector<uint32_t> compile_args_vec, int device_id) {

tt_metal::KernelID unary_reader_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/test_compile_args.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/test_compile_args.cpp",
core,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_1, .noc = tt_metal::NOC::RISCV_1_default, .compile_args = compile_args_vec});


tt_metal::KernelID unary_writer_kernel = tt_metal::CreateDataMovementKernel(
program, "tt_metal/kernels/dataflow/blank.cpp",
program, "tests/tt_metal/tt_metal/test_kernels/dataflow/blank.cpp",
core,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_0, .noc = tt_metal::NOC::RISCV_0_default});

Expand All @@ -50,7 +50,7 @@ bool test_compile_args(std::vector<uint32_t> compile_args_vec, int device_id) {
};

auto eltwise_unary_kernel = tt_metal::CreateComputeKernel(
program, "tt_metal/kernels/compute/blank.cpp",
program, "tests/tt_metal/tt_metal/test_kernels/compute/blank.cpp",
core, tt_metal::ComputeConfig{.compile_args = compute_args});

////////////////////////////////////////////////////////////////////////////
Expand Down
6 changes: 3 additions & 3 deletions tests/tt_metal/tt_metal/test_compile_program.cpp
View file
Original file line number Diff line number Diff line change
Expand Up @@ -114,13 +114,13 @@ Program create_program(Device *device, const ProgramAttributes &program_attribut

auto unary_reader_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/reader_unary_push_4.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/reader_unary_push_4.cpp",
core,
tt_metal::DataMovementConfig{.processor = program_attributes.reader_processor, .noc = program_attributes.reader_noc});

auto unary_writer_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/writer_unary.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/writer_unary.cpp",
core,
tt_metal::DataMovementConfig{.processor = program_attributes.writer_processor, .noc = program_attributes.writer_noc});

Expand All @@ -130,7 +130,7 @@ Program create_program(Device *device, const ProgramAttributes &program_attribut

auto eltwise_unary_kernel = tt_metal::CreateComputeKernel(
program,
"tt_metal/kernels/compute/eltwise_copy_3m.cpp",
"tests/tt_metal/tt_metal/test_kernels/compute/eltwise_copy_3m.cpp",
core,
tt_metal::ComputeConfig{
.math_fidelity = program_attributes.math_fidelity,
Expand Down
6 changes: 3 additions & 3 deletions tests/tt_metal/tt_metal/test_compile_sets_kernel_binaries.cpp
View file
Original file line number Diff line number Diff line change
Expand Up @@ -86,13 +86,13 @@ int main(int argc, char **argv) {

auto unary_reader_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/reader_unary_push_4.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/reader_unary_push_4.cpp",
core,
DataMovementConfig{.processor = DataMovementProcessor::RISCV_1, .noc = NOC::RISCV_1_default});

auto unary_writer_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/writer_unary.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/writer_unary.cpp",
core,
DataMovementConfig{.processor = DataMovementProcessor::RISCV_0, .noc = NOC::RISCV_0_default});

Expand All @@ -102,7 +102,7 @@ int main(int argc, char **argv) {

auto eltwise_unary_kernel = tt_metal::CreateComputeKernel(
program,
"tt_metal/kernels/compute/eltwise_copy_3m.cpp",
"tests/tt_metal/tt_metal/test_kernels/compute/eltwise_copy_3m.cpp",
core,
tt_metal::ComputeConfig{.compile_args = compute_kernel_args}
);
Expand Down
6 changes: 3 additions & 3 deletions tests/tt_metal/tt_metal/test_core_range_set.cpp
View file
Original file line number Diff line number Diff line change
Expand Up @@ -105,13 +105,13 @@ bool test_program_specified_with_core_range_set(tt_metal::Device *device, tt_met

auto unary_reader_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/reader_unary_push_4.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/reader_unary_push_4.cpp",
core_range_set,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_1, .noc = tt_metal::NOC::RISCV_1_default});

auto unary_writer_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/writer_unary.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/writer_unary.cpp",
core_range_set,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_0, .noc = tt_metal::NOC::RISCV_0_default});

Expand All @@ -122,7 +122,7 @@ bool test_program_specified_with_core_range_set(tt_metal::Device *device, tt_met

auto eltwise_unary_kernel = tt_metal::CreateComputeKernel(
program,
"tt_metal/kernels/compute/eltwise_copy_3m.cpp",
"tests/tt_metal/tt_metal/test_kernels/compute/eltwise_copy_3m.cpp",
core_range_set,
tt_metal::ComputeConfig{.compile_args = compute_kernel_args}
);
Expand Down
6 changes: 3 additions & 3 deletions tests/tt_metal/tt_metal/test_datacopy.cpp
View file
Original file line number Diff line number Diff line change
Expand Up @@ -77,13 +77,13 @@ int main(int argc, char **argv) {

auto unary_reader_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/reader_unary_push_4.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/reader_unary_push_4.cpp",
core,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_1, .noc = tt_metal::NOC::RISCV_1_default});

auto unary_writer_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/writer_unary.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/writer_unary.cpp",
core,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_0, .noc = tt_metal::NOC::RISCV_0_default});

Expand All @@ -93,7 +93,7 @@ int main(int argc, char **argv) {

auto eltwise_unary_kernel = tt_metal::CreateComputeKernel(
program,
"tt_metal/kernels/compute/eltwise_copy_3m.cpp",
"tests/tt_metal/tt_metal/test_kernels/compute/eltwise_copy_3m.cpp",
core,
tt_metal::ComputeConfig{.compile_args = compute_kernel_args}
);
Expand Down
6 changes: 3 additions & 3 deletions tests/tt_metal/tt_metal/test_datacopy_bfp8b.cpp
View file
Original file line number Diff line number Diff line change
Expand Up @@ -69,13 +69,13 @@ int main(int argc, char **argv) {

auto unary_reader_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/reader_unary.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/reader_unary.cpp",
core,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_1, .noc = tt_metal::NOC::RISCV_1_default});

auto unary_writer_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/writer_unary.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/writer_unary.cpp",
core,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_0, .noc = tt_metal::NOC::RISCV_0_default});

Expand All @@ -85,7 +85,7 @@ int main(int argc, char **argv) {

auto eltwise_unary_kernel = tt_metal::CreateComputeKernel(
program,
"tt_metal/kernels/compute/eltwise_copy_3m.cpp",
"tests/tt_metal/tt_metal/test_kernels/compute/eltwise_copy_3m.cpp",
core,
tt_metal::ComputeConfig{.compile_args = compute_kernel_args}
);
Expand Down
6 changes: 3 additions & 3 deletions tests/tt_metal/tt_metal/test_datacopy_multi_core_multi_dram.cpp
View file
Original file line number Diff line number Diff line change
Expand Up @@ -141,13 +141,13 @@ std::tuple<tt_metal::Program, tt_metal::KernelID, tt_metal::KernelID> create_pro

auto reader_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/reader_copy_tile_layout.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/reader_copy_tile_layout.cpp",
all_cores,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_1, .noc = tt_metal::NOC::RISCV_1_default});

auto writer_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/writer_copy_tile_layout.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/writer_copy_tile_layout.cpp",
all_cores,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_0, .noc = tt_metal::NOC::RISCV_0_default});

Expand All @@ -158,7 +158,7 @@ std::tuple<tt_metal::Program, tt_metal::KernelID, tt_metal::KernelID> create_pro

auto compute_kernel = tt_metal::CreateComputeKernel(
program,
"tt_metal/kernels/compute/eltwise_copy_block.cpp",
"tests/tt_metal/tt_metal/test_kernels/compute/eltwise_copy_block.cpp",
all_cores,
tt_metal::ComputeConfig{.compile_args = compute_kernel_args}
);
Expand Down
6 changes: 3 additions & 3 deletions tests/tt_metal/tt_metal/test_datacopy_output_in_l1.cpp
View file
Original file line number Diff line number Diff line change
Expand Up @@ -75,13 +75,13 @@ int main(int argc, char **argv) {

auto unary_reader_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/reader_unary_push_4.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/reader_unary_push_4.cpp",
core,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_1, .noc = tt_metal::NOC::RISCV_1_default});

auto unary_writer_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/writer_unary.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/writer_unary.cpp",
core,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_0, .noc = tt_metal::NOC::RISCV_0_default});

Expand All @@ -91,7 +91,7 @@ int main(int argc, char **argv) {

auto eltwise_unary_kernel = tt_metal::CreateComputeKernel(
program,
"tt_metal/kernels/compute/eltwise_copy_3m.cpp",
"tests/tt_metal/tt_metal/test_kernels/compute/eltwise_copy_3m.cpp",
core,
tt_metal::ComputeConfig{.compile_args = compute_kernel_args}
);
Expand Down
4 changes: 2 additions & 2 deletions tests/tt_metal/tt_metal/test_dataflow_cb.cpp
View file
Original file line number Diff line number Diff line change
Expand Up @@ -80,13 +80,13 @@ int main(int argc, char **argv) {

auto reader_cb_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/reader_cb_test.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/reader_cb_test.cpp",
core,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_1, .noc = tt_metal::NOC::RISCV_1_default, .compile_args = reader_cb_kernel_args});

auto writer_cb_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/writer_cb_test.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/writer_cb_test.cpp",
core,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_0, .noc = tt_metal::NOC::RISCV_0_default, .compile_args = writer_cb_kernel_args});

Expand Down
2 changes: 1 addition & 1 deletion tests/tt_metal/tt_metal/test_dram_copy_sticks_multi_core.cpp
View file
Original file line number Diff line number Diff line change
Expand Up @@ -74,7 +74,7 @@ int main(int argc, char **argv) {
}
auto unary_reader_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/dram_copy_sticks.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/dram_copy_sticks.cpp",
all_cores,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_1, .noc = tt_metal::NOC::RISCV_1_default});

Expand Down
4 changes: 2 additions & 2 deletions tests/tt_metal/tt_metal/test_dram_loopback_multi_core.cpp
View file
Original file line number Diff line number Diff line change
Expand Up @@ -85,14 +85,14 @@ int main(int argc, char **argv) {
// Loader (producer kernel) running on BRISC on logical core {0, 0}
auto producer_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/dram_loader_sync.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/dram_loader_sync.cpp",
loader_logical_core,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_0, .noc = tt_metal::NOC::RISCV_0_default});

// Writer (consumer kernel) running on NCRISC on logical core {0, 1}
auto consumer_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/remote_read_remote_write_sync.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/remote_read_remote_write_sync.cpp",
writer_logical_core,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_1, .noc = tt_metal::NOC::RISCV_1_default});

Expand Down
4 changes: 2 additions & 2 deletions tests/tt_metal/tt_metal/test_dram_loopback_multi_core_db.cpp
View file
Original file line number Diff line number Diff line change
Expand Up @@ -99,14 +99,14 @@ int main(int argc, char **argv) {
// Loader (producer kernel) running on BRISC on logical core {0, 0}
auto producer_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/dram_loader_sync_db.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/dram_loader_sync_db.cpp",
loader_logical_core,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_0, .noc = tt_metal::NOC::RISCV_0_default});

// Writer (consumer kernel) running on NCRISC on logical core {0, 1}
auto consumer_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/remote_read_remote_write_sync_db.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/remote_read_remote_write_sync_db.cpp",
writer_logical_core,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_1, .noc = tt_metal::NOC::RISCV_1_default});

Expand Down
2 changes: 1 addition & 1 deletion tests/tt_metal/tt_metal/test_dram_loopback_single_core.cpp
View file
Original file line number Diff line number Diff line change
Expand Up @@ -57,7 +57,7 @@ int main(int argc, char **argv) {

auto dram_copy_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/dram_copy.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/dram_copy.cpp",
core,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_0, .noc = tt_metal::NOC::RISCV_0_default});

Expand Down
2 changes: 1 addition & 1 deletion tests/tt_metal/tt_metal/test_dram_loopback_single_core_db.cpp
View file
Original file line number Diff line number Diff line change
Expand Up @@ -59,7 +59,7 @@ int main(int argc, char **argv) {

auto dram_copy_kernel = tt_metal::CreateDataMovementKernel(
program,
"tt_metal/kernels/dataflow/dram_copy_db.cpp",
"tests/tt_metal/tt_metal/test_kernels/dataflow/dram_copy_db.cpp",
core,
tt_metal::DataMovementConfig{.processor = tt_metal::DataMovementProcessor::RISCV_0, .noc = tt_metal::NOC::RISCV_0_default});

Expand Down
Loading

0 comments on commit 0a8950e

Please sign in to comment.