Untitled
unknown
plain_text
14 days ago
56 kB
8
Indexable
build/programming_examples/add_2_integers_in_compute
Device | INFO | Opening user mode device driver
Detecting chips (found 1)
2025-03-05 16:55:40.328 | INFO | SiliconDriver - Opened PCI device 0; KMD version: 1.30.0, IOMMU: disabled
2025-03-05 16:55:40.330 | INFO | SiliconDriver - Detected PCI devices: [0]
2025-03-05 16:55:40.330 | INFO | SiliconDriver - Using local chip ids: {0} and remote chip ids {}
Metal | INFO | Initializing device 0. Program cache is NOT enabled
Metal | INFO | AI CLK for device 0 is: 1000 MHz
BuildKernels | INFO | ncrisc compile failure -- cmd: cd /home/jush/tt-metal-latest/built/9b9282ad48/4672/firmware/ncrisc/ && /home/jush/tt-metal-latest/runtime/sfpi/compiler/bin/riscv32-unknown-elf-g++ -Os -mcpu=tt-gs -std=c++17 -flto -ffast-math -fno-use-cxa-atexit -fno-exceptions -Wall -Werror -Wno-unknown-pragmas -Wno-deprecated-declarations -Wno-error=multistatement-macros -Wno-error=parentheses -Wno-error=unused-but-set-variable -Wno-unused-variable -Wno-unused-function -fno-tree-loop-distribute-patterns -I. -I.. -I/home/jush/tt-metal-latest/ -I/home/jush/tt-metal-latest/ttnn -I/home/jush/tt-metal-latest/tt_metal -I/home/jush/tt-metal-latest/tt_metal/include -I/home/jush/tt-metal-latest/tt_metal/hw/inc -I/home/jush/tt-metal-latest/tt_metal/hostdevcommon/api -I/home/jush/tt-metal-latest/tt_metal/hw/inc/debug -I/home/jush/tt-metal-latest/tt_metal/hw/inc/grayskull -I/home/jush/tt-metal-latest/tt_metal/hw/inc/grayskull/grayskull_defines -I/home/jush/tt-metal-latest/tt_metal/hw/inc/grayskull/noc -I/home/jush/tt-metal-latest/tt_metal/hw/ckernels/grayskull/metal/common -I/home/jush/tt-metal-latest/tt_metal/hw/ckernels/grayskull/metal/llk_io -I/home/jush/tt-metal-latest/tt_metal/third_party/tt_llk/tt_llk_grayskull/common/inc -I/home/jush/tt-metal-latest/tt_metal/api/grayskull -I/home/jush/tt-metal-latest/tt_metal/api/grayskull/tt-metalium -I/home/jush/tt-metal-latest/tt_metal/api/tt-metalium/ -I/home/jush/tt-metal-latest/tt_metal/api/ -I/home/jush/tt-metal-latest/tt_metal/third_party/tt_llk/tt_llk_grayskull/llk_lib -I /home/jush/tt-metal-latest/tt_metal/hw/firmware/src -I /home/jush/tt-metal-latest/tt_metal/hw/ckernels/grayskull/metal/common -I /home/jush/tt-metal-latest/tt_metal/hw/ckernels/grayskull/metal/llk_io -c -o ncrisc.o /home/jush/tt-metal-latest/tt_metal/hw/firmware/src/ncrisc.cc -DARCH_GRAYSKULL -DIS_NOT_POW2_NUM_L1_BANKS=1 -DLOG_BASE_2_OF_NUM_DRAM_BANKS=3 -DNUM_DRAM_BANKS=8 -DNUM_L1_BANKS=94 -DPCIE_NOC_X=0 -DPCIE_NOC_Y=4 -DTENSIX_FIRMWARE -DLOCAL_MEM_EN=0 -DCOMPILE_FOR_NCRISC -DFW_BUILD -DDISPATCH_MESSAGE_ADDR=100592
In file included from /home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:30,
from /home/jush/tt-metal-latest/tt_metal/hw/firmware/src/ncrisc.cc:13:
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h: In member function 'void InterleavedAddrGenFast<DRAM, tile_hw>::noc_async_read_tile(uint32_t, uint32_t, uint32_t, uint8_t) const':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:361:13: error: 'inc_noc_counter_val' was not declared in this scope
361 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:361:33: error: 'proc_type' was not declared in this scope
361 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:361:44: error: 'NocBarrierType' has not been declared
361 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h: In member function 'void InterleavedAddrGenFast<DRAM, tile_hw>::noc_async_write_tile(uint32_t, uint32_t, uint8_t) const':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:393:13: error: 'inc_noc_counter_val' was not declared in this scope
393 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:393:33: error: 'proc_type' was not declared in this scope
393 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:393:44: error: 'NocBarrierType' has not been declared
393 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:394:44: error: 'NocBarrierType' has not been declared
394 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_ACKED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h: In member function 'void InterleavedPow2AddrGenFast<DRAM>::noc_async_read_page(uint32_t, uint32_t, uint32_t, uint8_t) const':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:461:13: error: 'inc_noc_counter_val' was not declared in this scope
461 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:461:33: error: 'proc_type' was not declared in this scope
461 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:461:44: error: 'NocBarrierType' has not been declared
461 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h: In member function 'void InterleavedPow2AddrGenFast<DRAM>::noc_async_read_partial_page(uint32_t, uint32_t, uint32_t, uint32_t, uint8_t) const':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:495:13: error: 'inc_noc_counter_val' was not declared in this scope
495 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:495:33: error: 'proc_type' was not declared in this scope
495 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:495:44: error: 'NocBarrierType' has not been declared
495 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h: In member function 'void InterleavedPow2AddrGenFast<DRAM>::noc_async_write_page(uint32_t, uint32_t, uint32_t, uint32_t, uint8_t) const':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:532:13: error: 'inc_noc_counter_val' was not declared in this scope
532 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:532:33: error: 'proc_type' was not declared in this scope
532 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:532:44: error: 'NocBarrierType' has not been declared
532 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:533:44: error: 'NocBarrierType' has not been declared
533 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_ACKED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_read_one_packet(uint64_t, uint32_t, uint32_t, uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:470:9: error: 'inc_noc_counter_val' was not declared in this scope
470 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:470:29: error: 'proc_type' was not declared in this scope
470 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:470:40: error: 'NocBarrierType' has not been declared
470 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:470:74: error: left operand of comma operator has no effect [-Werror=unused-value]
470 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_read(uint64_t, uint32_t, uint32_t, uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:508:37: error: ISO C++ forbids comparison between pointer and integer [-fpermissive]
508 | ncrisc_noc_fast_read_any_len<noc_mode>(noc, read_cmd_buf, src_noc_addr, dst_local_l1_addr, size);
| ~~~~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_read_one_packet_with_state(uint32_t, uint32_t, uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:572:13: error: 'inc_noc_counter_val' was not declared in this scope
572 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:572:33: error: 'proc_type' was not declared in this scope
572 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:572:44: error: 'NocBarrierType' has not been declared
572 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_read_with_state(uint32_t, uint32_t, uint32_t, uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:640:17: error: 'inc_noc_counter_val' was not declared in this scope
640 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:640:37: error: 'proc_type' was not declared in this scope
640 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:640:48: error: 'NocBarrierType' has not been declared
640 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:658:13: error: 'inc_noc_counter_val' was not declared in this scope
658 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:658:33: error: 'proc_type' was not declared in this scope
658 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:658:44: error: 'NocBarrierType' has not been declared
658 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_read_inc_num_issued(uint32_t, uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:670:9: error: 'inc_noc_counter_val' was not declared in this scope
670 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, num_issued_reads_inc);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:670:29: error: 'proc_type' was not declared in this scope
670 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, num_issued_reads_inc);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:670:40: error: 'NocBarrierType' has not been declared
670 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, num_issued_reads_inc);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:670:74: error: left operand of comma operator has no effect [-Werror=unused-value]
670 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, num_issued_reads_inc);
| ^~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_write_one_packet(uint32_t, uint64_t, uint32_t, uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:706:9: error: 'inc_noc_counter_val' was not declared in this scope
706 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:706:29: error: 'proc_type' was not declared in this scope
706 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:706:40: error: 'NocBarrierType' has not been declared
706 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:706:85: error: left operand of comma operator has no effect [-Werror=unused-value]
706 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:707:40: error: 'NocBarrierType' has not been declared
707 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_ACKED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:707:80: error: left operand of comma operator has no effect [-Werror=unused-value]
707 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_ACKED>(noc, 1);
| ^~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_write_multicast_one_packet(uint32_t, uint64_t, uint32_t, uint32_t, bool, bool, uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:750:9: error: 'inc_noc_counter_val' was not declared in this scope
750 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:750:29: error: 'proc_type' was not declared in this scope
750 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:750:40: error: 'NocBarrierType' has not been declared
750 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:750:85: error: left operand of comma operator has no effect [-Werror=unused-value]
750 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:751:40: error: 'NocBarrierType' has not been declared
751 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_ACKED>(noc, num_dests);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:751:80: error: left operand of comma operator has no effect [-Werror=unused-value]
751 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_ACKED>(noc, num_dests);
| ^~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_write_one_packet_with_state(uint32_t, uint32_t, uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:803:13: error: 'inc_noc_counter_val' was not declared in this scope
803 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:803:33: error: 'proc_type' was not declared in this scope
803 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:803:44: error: 'NocBarrierType' has not been declared
803 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:804:44: error: 'NocBarrierType' has not been declared
804 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_ACKED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_read_barrier(uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1169:17: error: 'ncrisc_dynamic_noc_reads_flushed' was not declared in this scope; did you mean 'ncrisc_noc_reads_flushed'?
1169 | while (!ncrisc_dynamic_noc_reads_flushed(noc)) {
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
| ncrisc_noc_reads_flushed
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_write_barrier(uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1191:60: error: no matching function for call to 'ncrisc_dynamic_noc_nonposted_writes_flushed(uint8_t&)'
1191 | while (!ncrisc_dynamic_noc_nonposted_writes_flushed(noc)) {
| ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~
In file included from /home/jush/tt-metal-latest/tt_metal/hw/inc/risc_common.h:145,
from /home/jush/tt-metal-latest/tt_metal/hw/firmware/src/ncrisc.cc:7:
/home/jush/tt-metal-latest/tt_metal/hw/inc/grayskull/noc_nonblocking_api.h:222:44: note: candidate: 'template<long unsigned int proc_type> bool ncrisc_dynamic_noc_nonposted_writes_flushed(uint32_t)'
222 | inline __attribute__((always_inline)) bool ncrisc_dynamic_noc_nonposted_writes_flushed(uint32_t noc) {
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/grayskull/noc_nonblocking_api.h:222:44: note: template argument deduction/substitution failed:
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1191:60: note: couldn't deduce template parameter 'proc_type'
1191 | while (!ncrisc_dynamic_noc_nonposted_writes_flushed(noc)) {
| ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_writes_flushed(uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1210:17: error: 'ncrisc_dynamic_noc_nonposted_writes_sent' was not declared in this scope; did you mean 'ncrisc_dynamic_noc_nonposted_writes_flushed'?
1210 | while (!ncrisc_dynamic_noc_nonposted_writes_sent(noc)) {
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
| ncrisc_dynamic_noc_nonposted_writes_flushed
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_posted_writes_flushed(uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1229:17: error: 'ncrisc_dynamic_noc_posted_writes_sent' was not declared in this scope; did you mean 'ncrisc_noc_nonposted_writes_sent'?
1229 | while (!ncrisc_dynamic_noc_posted_writes_sent(noc)) {
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
| ncrisc_noc_nonposted_writes_sent
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_atomic_barrier(uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1251:17: error: 'ncrisc_dynamic_noc_nonposted_atomics_flushed' was not declared in this scope; did you mean 'ncrisc_dynamic_noc_nonposted_writes_flushed'?
1251 | while (!ncrisc_dynamic_noc_nonposted_atomics_flushed(noc_idx)) {
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
| ncrisc_dynamic_noc_nonposted_writes_flushed
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_full_barrier(uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1274:17: error: 'ncrisc_dynamic_noc_reads_flushed' was not declared in this scope; did you mean 'ncrisc_noc_reads_flushed'?
1274 | while (!ncrisc_dynamic_noc_reads_flushed(noc_idx));
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
| ncrisc_noc_reads_flushed
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1276:17: error: 'ncrisc_dynamic_noc_nonposted_writes_sent' was not declared in this scope; did you mean 'ncrisc_dynamic_noc_nonposted_writes_flushed'?
1276 | while (!ncrisc_dynamic_noc_nonposted_writes_sent(noc_idx));
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
| ncrisc_dynamic_noc_nonposted_writes_flushed
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1278:60: error: no matching function for call to 'ncrisc_dynamic_noc_nonposted_writes_flushed(uint8_t&)'
1278 | while (!ncrisc_dynamic_noc_nonposted_writes_flushed(noc_idx));
| ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/grayskull/noc_nonblocking_api.h:222:44: note: candidate: 'template<long unsigned int proc_type> bool ncrisc_dynamic_noc_nonposted_writes_flushed(uint32_t)'
222 | inline __attribute__((always_inline)) bool ncrisc_dynamic_noc_nonposted_writes_flushed(uint32_t noc) {
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/grayskull/noc_nonblocking_api.h:222:44: note: template argument deduction/substitution failed:
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1278:60: note: couldn't deduce template parameter 'proc_type'
1278 | while (!ncrisc_dynamic_noc_nonposted_writes_flushed(noc_idx));
| ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1280:17: error: 'ncrisc_dynamic_noc_nonposted_atomics_flushed' was not declared in this scope; did you mean 'ncrisc_dynamic_noc_nonposted_writes_flushed'?
1280 | while (!ncrisc_dynamic_noc_nonposted_atomics_flushed(noc_idx));
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
| ncrisc_dynamic_noc_nonposted_writes_flushed
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1282:17: error: 'ncrisc_dynamic_noc_posted_writes_sent' was not declared in this scope; did you mean 'ncrisc_noc_nonposted_writes_sent'?
1282 | while (!ncrisc_dynamic_noc_posted_writes_sent(noc_idx));
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
| ncrisc_noc_nonposted_writes_sent
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_read_tile_dram_sharded_with_state(uint32_t, uint32_t, uint32_t, uint32_t, uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1498:9: error: 'inc_noc_counter_val' was not declared in this scope
1498 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1498:29: error: 'proc_type' was not declared in this scope
1498 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1498:40: error: 'NocBarrierType' has not been declared
1498 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1498:74: error: left operand of comma operator has no effect [-Werror=unused-value]
1498 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~
cc1plus: all warnings being treated as errors
BuildKernels | INFO | brisc compile failure -- cmd: cd /home/jush/tt-metal-latest/built/9b9282ad48/4672/firmware/brisc/ && /home/jush/tt-metal-latest/runtime/sfpi/compiler/bin/riscv32-unknown-elf-g++ -Os -mcpu=tt-gs -std=c++17 -flto -ffast-math -fno-use-cxa-atexit -fno-exceptions -Wall -Werror -Wno-unknown-pragmas -Wno-deprecated-declarations -Wno-error=multistatement-macros -Wno-error=parentheses -Wno-error=unused-but-set-variable -Wno-unused-variable -Wno-unused-function -fno-tree-loop-distribute-patterns -I. -I.. -I/home/jush/tt-metal-latest/ -I/home/jush/tt-metal-latest/ttnn -I/home/jush/tt-metal-latest/tt_metal -I/home/jush/tt-metal-latest/tt_metal/include -I/home/jush/tt-metal-latest/tt_metal/hw/inc -I/home/jush/tt-metal-latest/tt_metal/hostdevcommon/api -I/home/jush/tt-metal-latest/tt_metal/hw/inc/debug -I/home/jush/tt-metal-latest/tt_metal/hw/inc/grayskull -I/home/jush/tt-metal-latest/tt_metal/hw/inc/grayskull/grayskull_defines -I/home/jush/tt-metal-latest/tt_metal/hw/inc/grayskull/noc -I/home/jush/tt-metal-latest/tt_metal/hw/ckernels/grayskull/metal/common -I/home/jush/tt-metal-latest/tt_metal/hw/ckernels/grayskull/metal/llk_io -I/home/jush/tt-metal-latest/tt_metal/third_party/tt_llk/tt_llk_grayskull/common/inc -I/home/jush/tt-metal-latest/tt_metal/api/grayskull -I/home/jush/tt-metal-latest/tt_metal/api/grayskull/tt-metalium -I/home/jush/tt-metal-latest/tt_metal/api/tt-metalium/ -I/home/jush/tt-metal-latest/tt_metal/api/ -I/home/jush/tt-metal-latest/tt_metal/third_party/tt_llk/tt_llk_grayskull/llk_lib -I /home/jush/tt-metal-latest/tt_metal/hw/firmware/src -I /home/jush/tt-metal-latest/tt_metal/hw/ckernels/grayskull/metal/common -I /home/jush/tt-metal-latest/tt_metal/hw/ckernels/grayskull/metal/llk_io -c -o brisc.o /home/jush/tt-metal-latest/tt_metal/hw/firmware/src/brisc.cc -DARCH_GRAYSKULL -DIS_NOT_POW2_NUM_L1_BANKS=1 -DLOG_BASE_2_OF_NUM_DRAM_BANKS=3 -DNUM_DRAM_BANKS=8 -DNUM_L1_BANKS=94 -DPCIE_NOC_X=0 -DPCIE_NOC_Y=4 -DTENSIX_FIRMWARE -DLOCAL_MEM_EN=0 -DCOMPILE_FOR_BRISC -DFW_BUILD -DDISPATCH_MESSAGE_ADDR=100592
In file included from /home/jush/tt-metal-latest/tt_metal/tools/profiler/kernel_profiler.hpp:12,
from /home/jush/tt-metal-latest/tt_metal/hw/firmware/src/brisc.cc:20:
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h: In member function 'void InterleavedAddrGenFast<DRAM, tile_hw>::noc_async_read_tile(uint32_t, uint32_t, uint32_t, uint8_t) const':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:361:13: error: 'inc_noc_counter_val' was not declared in this scope
361 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:361:33: error: 'proc_type' was not declared in this scope
361 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:361:44: error: 'NocBarrierType' has not been declared
361 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h: In member function 'void InterleavedAddrGenFast<DRAM, tile_hw>::noc_async_write_tile(uint32_t, uint32_t, uint8_t) const':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:393:13: error: 'inc_noc_counter_val' was not declared in this scope
393 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:393:33: error: 'proc_type' was not declared in this scope
393 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:393:44: error: 'NocBarrierType' has not been declared
393 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:394:44: error: 'NocBarrierType' has not been declared
394 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_ACKED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h: In member function 'void InterleavedPow2AddrGenFast<DRAM>::noc_async_read_page(uint32_t, uint32_t, uint32_t, uint8_t) const':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:461:13: error: 'inc_noc_counter_val' was not declared in this scope
461 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:461:33: error: 'proc_type' was not declared in this scope
461 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:461:44: error: 'NocBarrierType' has not been declared
461 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h: In member function 'void InterleavedPow2AddrGenFast<DRAM>::noc_async_read_partial_page(uint32_t, uint32_t, uint32_t, uint32_t, uint8_t) const':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:495:13: error: 'inc_noc_counter_val' was not declared in this scope
495 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:495:33: error: 'proc_type' was not declared in this scope
495 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:495:44: error: 'NocBarrierType' has not been declared
495 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h: In member function 'void InterleavedPow2AddrGenFast<DRAM>::noc_async_write_page(uint32_t, uint32_t, uint32_t, uint32_t, uint8_t) const':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:532:13: error: 'inc_noc_counter_val' was not declared in this scope
532 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:532:33: error: 'proc_type' was not declared in this scope
532 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:532:44: error: 'NocBarrierType' has not been declared
532 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api_addrgen.h:533:44: error: 'NocBarrierType' has not been declared
533 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_ACKED>(noc, 1);
| ^~~~~~~~~~~~~~
In file included from /home/jush/tt-metal-latest/tt_metal/hw/inc/remote_circular_buffer_api.h:11,
from /home/jush/tt-metal-latest/tt_metal/hw/inc/circular_buffer_init.h:11,
from /home/jush/tt-metal-latest/tt_metal/hw/firmware/src/brisc.cc:24:
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_read_one_packet(uint64_t, uint32_t, uint32_t, uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:470:9: error: 'inc_noc_counter_val' was not declared in this scope
470 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:470:29: error: 'proc_type' was not declared in this scope
470 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:470:40: error: 'NocBarrierType' has not been declared
470 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:470:74: error: left operand of comma operator has no effect [-Werror=unused-value]
470 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_read(uint64_t, uint32_t, uint32_t, uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:508:37: error: ISO C++ forbids comparison between pointer and integer [-fpermissive]
508 | ncrisc_noc_fast_read_any_len<noc_mode>(noc, read_cmd_buf, src_noc_addr, dst_local_l1_addr, size);
| ~~~~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_read_one_packet_with_state(uint32_t, uint32_t, uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:572:13: error: 'inc_noc_counter_val' was not declared in this scope
572 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:572:33: error: 'proc_type' was not declared in this scope
572 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:572:44: error: 'NocBarrierType' has not been declared
572 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_read_with_state(uint32_t, uint32_t, uint32_t, uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:640:17: error: 'inc_noc_counter_val' was not declared in this scope
640 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:640:37: error: 'proc_type' was not declared in this scope
640 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:640:48: error: 'NocBarrierType' has not been declared
640 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:658:13: error: 'inc_noc_counter_val' was not declared in this scope
658 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:658:33: error: 'proc_type' was not declared in this scope
658 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:658:44: error: 'NocBarrierType' has not been declared
658 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_read_inc_num_issued(uint32_t, uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:670:9: error: 'inc_noc_counter_val' was not declared in this scope
670 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, num_issued_reads_inc);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:670:29: error: 'proc_type' was not declared in this scope
670 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, num_issued_reads_inc);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:670:40: error: 'NocBarrierType' has not been declared
670 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, num_issued_reads_inc);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:670:74: error: left operand of comma operator has no effect [-Werror=unused-value]
670 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, num_issued_reads_inc);
| ^~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_write_one_packet(uint32_t, uint64_t, uint32_t, uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:706:9: error: 'inc_noc_counter_val' was not declared in this scope
706 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:706:29: error: 'proc_type' was not declared in this scope
706 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:706:40: error: 'NocBarrierType' has not been declared
706 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:706:85: error: left operand of comma operator has no effect [-Werror=unused-value]
706 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:707:40: error: 'NocBarrierType' has not been declared
707 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_ACKED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:707:80: error: left operand of comma operator has no effect [-Werror=unused-value]
707 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_ACKED>(noc, 1);
| ^~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_write_multicast_one_packet(uint32_t, uint64_t, uint32_t, uint32_t, bool, bool, uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:750:9: error: 'inc_noc_counter_val' was not declared in this scope
750 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:750:29: error: 'proc_type' was not declared in this scope
750 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:750:40: error: 'NocBarrierType' has not been declared
750 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:750:85: error: left operand of comma operator has no effect [-Werror=unused-value]
750 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:751:40: error: 'NocBarrierType' has not been declared
751 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_ACKED>(noc, num_dests);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:751:80: error: left operand of comma operator has no effect [-Werror=unused-value]
751 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_ACKED>(noc, num_dests);
| ^~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_write_one_packet_with_state(uint32_t, uint32_t, uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:803:13: error: 'inc_noc_counter_val' was not declared in this scope
803 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:803:33: error: 'proc_type' was not declared in this scope
803 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:803:44: error: 'NocBarrierType' has not been declared
803 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:804:44: error: 'NocBarrierType' has not been declared
804 | inc_noc_counter_val<proc_type, NocBarrierType::NONPOSTED_WRITES_ACKED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_read_barrier(uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1169:17: error: 'ncrisc_dynamic_noc_reads_flushed' was not declared in this scope; did you mean 'ncrisc_noc_reads_flushed'?
1169 | while (!ncrisc_dynamic_noc_reads_flushed(noc)) {
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
| ncrisc_noc_reads_flushed
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_write_barrier(uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1191:60: error: no matching function for call to 'ncrisc_dynamic_noc_nonposted_writes_flushed(uint8_t&)'
1191 | while (!ncrisc_dynamic_noc_nonposted_writes_flushed(noc)) {
| ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~
In file included from /home/jush/tt-metal-latest/tt_metal/hw/inc/risc_common.h:145,
from /home/jush/tt-metal-latest/tt_metal/hw/firmware/src/brisc.cc:10:
/home/jush/tt-metal-latest/tt_metal/hw/inc/grayskull/noc_nonblocking_api.h:222:44: note: candidate: 'template<long unsigned int proc_type> bool ncrisc_dynamic_noc_nonposted_writes_flushed(uint32_t)'
222 | inline __attribute__((always_inline)) bool ncrisc_dynamic_noc_nonposted_writes_flushed(uint32_t noc) {
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/grayskull/noc_nonblocking_api.h:222:44: note: template argument deduction/substitution failed:
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1191:60: note: couldn't deduce template parameter 'proc_type'
1191 | while (!ncrisc_dynamic_noc_nonposted_writes_flushed(noc)) {
| ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_writes_flushed(uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1210:17: error: 'ncrisc_dynamic_noc_nonposted_writes_sent' was not declared in this scope; did you mean 'ncrisc_dynamic_noc_nonposted_writes_flushed'?
1210 | while (!ncrisc_dynamic_noc_nonposted_writes_sent(noc)) {
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
| ncrisc_dynamic_noc_nonposted_writes_flushed
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_posted_writes_flushed(uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1229:17: error: 'ncrisc_dynamic_noc_posted_writes_sent' was not declared in this scope; did you mean 'ncrisc_noc_nonposted_writes_sent'?
1229 | while (!ncrisc_dynamic_noc_posted_writes_sent(noc)) {
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
| ncrisc_noc_nonposted_writes_sent
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_atomic_barrier(uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1251:17: error: 'ncrisc_dynamic_noc_nonposted_atomics_flushed' was not declared in this scope; did you mean 'ncrisc_dynamic_noc_nonposted_writes_flushed'?
1251 | while (!ncrisc_dynamic_noc_nonposted_atomics_flushed(noc_idx)) {
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
| ncrisc_dynamic_noc_nonposted_writes_flushed
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_full_barrier(uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1274:17: error: 'ncrisc_dynamic_noc_reads_flushed' was not declared in this scope; did you mean 'ncrisc_noc_reads_flushed'?
1274 | while (!ncrisc_dynamic_noc_reads_flushed(noc_idx));
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
| ncrisc_noc_reads_flushed
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1276:17: error: 'ncrisc_dynamic_noc_nonposted_writes_sent' was not declared in this scope; did you mean 'ncrisc_dynamic_noc_nonposted_writes_flushed'?
1276 | while (!ncrisc_dynamic_noc_nonposted_writes_sent(noc_idx));
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
| ncrisc_dynamic_noc_nonposted_writes_flushed
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1278:60: error: no matching function for call to 'ncrisc_dynamic_noc_nonposted_writes_flushed(uint8_t&)'
1278 | while (!ncrisc_dynamic_noc_nonposted_writes_flushed(noc_idx));
| ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/grayskull/noc_nonblocking_api.h:222:44: note: candidate: 'template<long unsigned int proc_type> bool ncrisc_dynamic_noc_nonposted_writes_flushed(uint32_t)'
222 | inline __attribute__((always_inline)) bool ncrisc_dynamic_noc_nonposted_writes_flushed(uint32_t noc) {
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/grayskull/noc_nonblocking_api.h:222:44: note: template argument deduction/substitution failed:
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1278:60: note: couldn't deduce template parameter 'proc_type'
1278 | while (!ncrisc_dynamic_noc_nonposted_writes_flushed(noc_idx));
| ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1280:17: error: 'ncrisc_dynamic_noc_nonposted_atomics_flushed' was not declared in this scope; did you mean 'ncrisc_dynamic_noc_nonposted_writes_flushed'?
1280 | while (!ncrisc_dynamic_noc_nonposted_atomics_flushed(noc_idx));
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
| ncrisc_dynamic_noc_nonposted_writes_flushed
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1282:17: error: 'ncrisc_dynamic_noc_posted_writes_sent' was not declared in this scope; did you mean 'ncrisc_noc_nonposted_writes_sent'?
1282 | while (!ncrisc_dynamic_noc_posted_writes_sent(noc_idx));
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
| ncrisc_noc_nonposted_writes_sent
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h: In function 'void noc_async_read_tile_dram_sharded_with_state(uint32_t, uint32_t, uint32_t, uint32_t, uint8_t)':
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1498:9: error: 'inc_noc_counter_val' was not declared in this scope
1498 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1498:29: error: 'proc_type' was not declared in this scope
1498 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1498:40: error: 'NocBarrierType' has not been declared
1498 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~~~~~~~~~~~~
/home/jush/tt-metal-latest/tt_metal/hw/inc/dataflow_api.h:1498:74: error: left operand of comma operator has no effect [-Werror=unused-value]
1498 | inc_noc_counter_val<proc_type, NocBarrierType::READS_NUM_ISSUED>(noc, 1);
| ^~~
cc1plus: all warnings being treated as errors
terminate called after throwing an instance of 'std::runtime_error'
what(): TT_THROW @ /home/jush/tt-metal-latest/tt_metal/jit_build/build.cpp:624: tt::exception
info:
brisc build failed
backtrace:
--- void tt::assert::tt_throw<std::__cxx11::basic_string<char, std::char_traits<char>, std::allocator<char> > >(char const*, int, char const*, char const*, fmt::v11::basic_format_string<char, fmt::v11::type_identity<std::__cxx11::basic_string<char, std::char_traits<char>, std::allocator<char> > const&>::type>, std::__cxx11::basic_string<char, std::char_traits<char>, std::allocator<char> > const&)
--- /home/jush/tt-metal-latest/build_Release/tt_metal/libtt_metal.so(+0x2907bf) [0x7b86352907bf]
--- tt::tt_metal::JitBuildState::compile_one(std::__cxx11::basic_string<char, std::char_traits<char>, std::allocator<char> > const&, std::__cxx11::basic_string<char, std::char_traits<char>, std::allocator<char> > const&, tt::tt_metal::JitBuildSettings const*, std::__cxx11::basic_string<char, std::char_traits<char>, std::allocator<char> > const&, std::__cxx11::basic_string<char, std::char_traits<char>, std::allocator<char> > const&) const
--- /home/jush/tt-metal-latest/build_Release/tt_metal/libtt_metal.so(+0x296632) [0x7b8635296632]
--- /home/jush/tt-metal-latest/build_Release/tt_metal/libtt_metal.so(+0x29659e) [0x7b863529659e]
--- /home/jush/tt-metal-latest/build_Release/tt_metal/libtt_metal.so(+0x1ecdca) [0x7b86351ecdca]
--- /usr/lib/libc.so.6(+0x97267) [0x7b86342a9267]
--- /usr/lib/libc.so.6(pthread_once+0x19) [0x7b86342a92d9]
--- /home/jush/tt-metal-latest/build_Release/tt_metal/libtt_metal.so(+0x26f520) [0x7b863526f520]
--- /home/jush/tt-metal-latest/build_Release/tt_metal/libtt_metal.so(+0x29633c) [0x7b863529633c]
--- /home/jush/tt-metal-latest/build_Release/tt_metal/libtt_metal.so(+0x29a8d9) [0x7b863529a8d9]
--- /home/jush/tt-metal-latest/build_Release/tt_metal/libtt_metal.so(+0x29927d) [0x7b863529927d]
--- /home/jush/tt-metal-latest/build_Release/tt_metal/libtt_metal.so(+0x298609) [0x7b8635298609]
--- /usr/lib/libstdc++.so.6(+0xe0bc4) [0x7b86344e0bc4]
--- /usr/lib/libc.so.6(+0x920bb) [0x7b86342a40bb]
--- /usr/lib/libc.so.6(+0x11238c) [0x7b863432438c]
AbortedEditor is loading...
Leave a Comment