Compiler Command: aoc --board de5a_net_e1 device/fft1d.cl -o bin/fft1d.aocx -v ========================================================================================================= *** Optimization Report *** Kernels that do not use any work-item built-in functions, such as get_global_id(), are compiled for single work-item execution (a task). Otherwise, a kernel is compiled as an ND-Range. For tasks, the compiler will attempt to pipeline every loop in the kernel to allow multiple iterations of the loop to execute concurrently. If some loops are not pipelined, or not pipelined well, you may not get good performance. For ND-Range kernels, the loops are not pipelined. Instead, they are built to accept multiple work-items simultaneously. Kernel throughput is usually reduced by the largest total number of iterations of nested loops. A large number of threads is usually required to efficiently utilize ND-Range kernels. ========================================================================================================= Kernel: fetch ========================================================================================================= The kernel is compiled as an ND-Range. The kernel has a required work-group size of (512, 1, 1). Loop Report: + Fully unrolled loop (file fft1d.cl line 157) Loop was fully unrolled due to "#pragma unroll" annotation. + Fully unrolled loop (file fft1d.cl line 164) | Loop was fully unrolled due to "#pragma unroll" annotation. | | |-+ Fully unrolled loop (file fft1d.cl line 69) Loop was fully unrolled due to "#pragma unroll" annotation. ========================================================================================================= Kernel: fft1d ========================================================================================================= The kernel is compiled for single work-item execution. The kernel has a required work-group size of (1, 1, 1). Loop Report: + Loop "Block3" (file fft1d.cl line 203) | Pipelined well. Successive iterations are launched every cycle. | | |-+ Fully unrolled loop (file fft_8.cl line 296) | Loop was fully unrolled due to "#pragma unroll" annotation. | | |-+ Fully unrolled loop (file fft_8.cl line 337) Loop was fully unrolled due to "#pragma unroll" annotation. ========================================================================================================= +--------------------------------------------------------------------+ ; Estimated Resource Usage Summary ; +----------------------------------------+---------------------------+ ; Resource + Usage ; +----------------------------------------+---------------------------+ ; Logic utilization ; 23% ; ; ALUTs ; 11% ; ; Dedicated logic registers ; 12% ; ; Memory blocks ; 27% ; ; DSP blocks ; 26% ; +----------------------------------------+---------------------------; System name: fft1d 2018.03.23.10:02:20 Info: Doing: qsys-script --quartus-project=top --script=kernel_system.tcl --Xmx512M --XX:+UseSerialGC 2018.03.23.10:02:25 Info: set_validation_property AUTOMATIC_VALIDATION false 2018.03.23.10:02:25 Info: add_instance clk_1x altera_clock_bridge 2018.03.23.10:02:25 Info: set_instance_parameter_value clk_1x EXPLICIT_CLOCK_RATE 0 2018.03.23.10:02:25 Info: set_instance_parameter_value clk_1x NUM_CLOCK_OUTPUTS 1 2018.03.23.10:02:25 Info: add_interface clock_reset clock sink 2018.03.23.10:02:25 Info: set_interface_property clock_reset EXPORT_OF clk_1x.in_clk 2018.03.23.10:02:25 Info: add_instance clk_2x altera_clock_bridge 2018.03.23.10:02:25 Info: set_instance_parameter_value clk_2x EXPLICIT_CLOCK_RATE 0 2018.03.23.10:02:25 Info: set_instance_parameter_value clk_2x NUM_CLOCK_OUTPUTS 1 2018.03.23.10:02:25 Info: add_interface clock_reset2x clock sink 2018.03.23.10:02:25 Info: set_interface_property clock_reset2x EXPORT_OF clk_2x.in_clk 2018.03.23.10:02:25 Info: add_instance clk_snoop altera_clock_bridge 2018.03.23.10:02:25 Info: set_instance_parameter_value clk_snoop EXPLICIT_CLOCK_RATE 0 2018.03.23.10:02:25 Info: set_instance_parameter_value clk_snoop NUM_CLOCK_OUTPUTS 1 2018.03.23.10:02:25 Info: add_interface cc_snoop_clk clock sink 2018.03.23.10:02:25 Info: set_interface_property cc_snoop_clk EXPORT_OF clk_snoop.in_clk 2018.03.23.10:02:25 Info: add_instance reset altera_reset_bridge 2018.03.23.10:02:25 Info: set_instance_parameter_value reset ACTIVE_LOW_RESET 1 2018.03.23.10:02:25 Info: set_instance_parameter_value reset SYNCHRONOUS_EDGES deassert 2018.03.23.10:02:25 Info: set_instance_parameter_value reset NUM_RESET_OUTPUTS 1 2018.03.23.10:02:25 Info: add_interface clock_reset_reset reset sink 2018.03.23.10:02:25 Info: set_interface_property clock_reset_reset EXPORT_OF reset.in_reset 2018.03.23.10:02:25 Info: add_connection clk_1x.out_clk reset.clk 2018.03.23.10:02:25 Info: add_instance fft1d_system fft1d_system 2018.03.23.10:02:26 Info: add_connection clk_1x.out_clk fft1d_system.clock_reset 2018.03.23.10:02:26 Info: add_connection clk_2x.out_clk fft1d_system.clock_reset2x 2018.03.23.10:02:26 Info: add_connection reset.out_reset fft1d_system.clock_reset_reset 2018.03.23.10:02:26 Info: add_instance kernel_mem0 altera_avalon_mm_bridge 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_mem0 DATA_WIDTH 512 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_mem0 SYMBOL_WIDTH 8 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_mem0 ADDRESS_WIDTH 32 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_mem0 USE_AUTO_ADDRESS_WIDTH 0 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_mem0 ADDRESS_UNITS SYMBOLS 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_mem0 MAX_BURST_SIZE 16 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_mem0 MAX_PENDING_RESPONSES 64 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_mem0 LINEWRAPBURSTS 0 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_mem0 PIPELINE_COMMAND 1 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_mem0 PIPELINE_RESPONSE 1 2018.03.23.10:02:26 Info: add_connection clk_1x.out_clk kernel_mem0.clk 2018.03.23.10:02:26 Info: add_connection reset.out_reset kernel_mem0.reset 2018.03.23.10:02:26 Info: add_interface kernel_mem0 avalon slave 2018.03.23.10:02:26 Info: set_interface_property kernel_mem0 EXPORT_OF kernel_mem0.m0 2018.03.23.10:02:26 Info: add_instance kernel_mem1 altera_avalon_mm_bridge 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_mem1 DATA_WIDTH 512 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_mem1 SYMBOL_WIDTH 8 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_mem1 ADDRESS_WIDTH 32 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_mem1 USE_AUTO_ADDRESS_WIDTH 0 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_mem1 ADDRESS_UNITS SYMBOLS 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_mem1 MAX_BURST_SIZE 16 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_mem1 MAX_PENDING_RESPONSES 64 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_mem1 LINEWRAPBURSTS 0 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_mem1 PIPELINE_COMMAND 1 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_mem1 PIPELINE_RESPONSE 1 2018.03.23.10:02:26 Info: add_connection clk_1x.out_clk kernel_mem1.clk 2018.03.23.10:02:26 Info: add_connection reset.out_reset kernel_mem1.reset 2018.03.23.10:02:26 Info: add_interface kernel_mem1 avalon slave 2018.03.23.10:02:26 Info: set_interface_property kernel_mem1 EXPORT_OF kernel_mem1.m0 2018.03.23.10:02:26 Info: add_connection fft1d_system.avm_memgmem0_DDR_port_0_0_rw kernel_mem0.s0 2018.03.23.10:02:26 Info: add_connection fft1d_system.avm_memgmem0_DDR_port_1_0_rw kernel_mem1.s0 2018.03.23.10:02:26 Info: add_instance kernel_irq altera_irq_bridge 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_irq IRQ_WIDTH 1 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_irq IRQ_N 0 2018.03.23.10:02:26 Info: add_interface kernel_irq irq sender 2018.03.23.10:02:26 Info: set_interface_property kernel_irq EXPORT_OF kernel_irq.sender0_irq 2018.03.23.10:02:26 Info: add_connection clk_1x.out_clk kernel_irq.clk 2018.03.23.10:02:26 Info: add_connection reset.out_reset kernel_irq.clk_reset 2018.03.23.10:02:26 Info: add_connection kernel_irq.receiver_irq fft1d_system.kernel_irq 2018.03.23.10:02:26 Info: add_instance kernel_cra altera_avalon_mm_bridge 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_cra DATA_WIDTH 64 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_cra SYMBOL_WIDTH 8 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_cra ADDRESS_WIDTH 30 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_cra USE_AUTO_ADDRESS_WIDTH 0 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_cra ADDRESS_UNITS SYMBOLS 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_cra MAX_BURST_SIZE 1 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_cra MAX_PENDING_RESPONSES 1 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_cra LINEWRAPBURSTS 0 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_cra PIPELINE_COMMAND 0 2018.03.23.10:02:26 Info: set_instance_parameter_value kernel_cra PIPELINE_RESPONSE 0 2018.03.23.10:02:26 Info: add_connection clk_1x.out_clk kernel_cra.clk 2018.03.23.10:02:26 Info: add_connection reset.out_reset kernel_cra.reset 2018.03.23.10:02:26 Info: add_interface avs_kernel_cra avalon slave 2018.03.23.10:02:26 Info: set_interface_property kernel_cra EXPORT_OF kernel_cra.s0 2018.03.23.10:02:26 Info: add_instance cra_root cra_ring_root 2018.03.23.10:02:26 Info: set_instance_parameter_value cra_root DATA_W 64 2018.03.23.10:02:26 Info: set_instance_parameter_value cra_root ADDR_W 4 2018.03.23.10:02:26 Info: set_instance_parameter_value cra_root ID_W 1 2018.03.23.10:02:26 Info: set_instance_parameter_value cra_root ROM_ENABLE 1 2018.03.23.10:02:26 Info: add_connection clk_1x.out_clk cra_root.clock 2018.03.23.10:02:26 Info: add_connection reset.out_reset cra_root.reset 2018.03.23.10:02:26 Info: add_connection kernel_cra.m0 cra_root.cra_slave 2018.03.23.10:02:26 Info: set_connection_parameter_value kernel_cra.m0/cra_root.cra_slave baseAddress 0x0 2018.03.23.10:02:26 Info: add_instance cra_ring_rom cra_ring_rom 2018.03.23.10:02:26 Info: set_instance_parameter_value cra_ring_rom DATA_W 64 2018.03.23.10:02:26 Info: set_instance_parameter_value cra_ring_rom RING_ADDR_W 4 2018.03.23.10:02:26 Info: set_instance_parameter_value cra_ring_rom ID_W 1 2018.03.23.10:02:26 Info: add_connection cra_root.ring_out cra_ring_rom.ring_in 2018.03.23.10:02:26 Info: add_connection clk_1x.out_clk cra_ring_rom.clock 2018.03.23.10:02:26 Info: add_connection reset.out_reset cra_ring_rom.reset 2018.03.23.10:02:26 Info: add_instance avs_fetch_cra_cra_ring cra_ring_node 2018.03.23.10:02:26 Info: set_instance_parameter_value avs_fetch_cra_cra_ring DATA_W 64 2018.03.23.10:02:26 Info: set_instance_parameter_value avs_fetch_cra_cra_ring RING_ADDR_W 4 2018.03.23.10:02:26 Info: set_instance_parameter_value avs_fetch_cra_cra_ring CRA_ADDR_W 4 2018.03.23.10:02:26 Info: set_instance_parameter_value avs_fetch_cra_cra_ring ID_W 1 2018.03.23.10:02:26 Info: set_instance_parameter_value avs_fetch_cra_cra_ring ID 0 2018.03.23.10:02:26 Info: add_connection clk_1x.out_clk avs_fetch_cra_cra_ring.clock 2018.03.23.10:02:26 Info: add_connection reset.out_reset avs_fetch_cra_cra_ring.reset 2018.03.23.10:02:26 Info: add_connection cra_ring_rom.ring_out avs_fetch_cra_cra_ring.ring_in 2018.03.23.10:02:26 Info: add_connection avs_fetch_cra_cra_ring.cra_master fft1d_system.avs_fetch_cra 2018.03.23.10:02:26 Info: set_connection_parameter_value avs_fetch_cra_cra_ring.cra_master/fft1d_system.avs_fetch_cra baseAddress 0x0 2018.03.23.10:02:26 Info: add_instance avs_fft1d_cra_cra_ring cra_ring_node 2018.03.23.10:02:26 Info: set_instance_parameter_value avs_fft1d_cra_cra_ring DATA_W 64 2018.03.23.10:02:26 Info: set_instance_parameter_value avs_fft1d_cra_cra_ring RING_ADDR_W 4 2018.03.23.10:02:26 Info: set_instance_parameter_value avs_fft1d_cra_cra_ring CRA_ADDR_W 4 2018.03.23.10:02:26 Info: set_instance_parameter_value avs_fft1d_cra_cra_ring ID_W 1 2018.03.23.10:02:26 Info: set_instance_parameter_value avs_fft1d_cra_cra_ring ID 1 2018.03.23.10:02:26 Info: add_connection clk_1x.out_clk avs_fft1d_cra_cra_ring.clock 2018.03.23.10:02:26 Info: add_connection reset.out_reset avs_fft1d_cra_cra_ring.reset 2018.03.23.10:02:26 Info: add_connection avs_fetch_cra_cra_ring.ring_out avs_fft1d_cra_cra_ring.ring_in 2018.03.23.10:02:26 Info: add_connection avs_fft1d_cra_cra_ring.cra_master fft1d_system.avs_fft1d_cra 2018.03.23.10:02:26 Info: set_connection_parameter_value avs_fft1d_cra_cra_ring.cra_master/fft1d_system.avs_fft1d_cra baseAddress 0x0 2018.03.23.10:02:26 Info: add_connection avs_fft1d_cra_cra_ring.ring_out cra_root.ring_in 2018.03.23.10:02:26 Info: add_instance acl_internal_snoop altera_avalon_st_adapter 2018.03.23.10:02:26 Info: set_instance_parameter_value acl_internal_snoop inBitsPerSymbol 33 2018.03.23.10:02:26 Info: set_instance_parameter_value acl_internal_snoop inUsePackets 0 2018.03.23.10:02:26 Info: set_instance_parameter_value acl_internal_snoop inDataWidth 33 2018.03.23.10:02:26 Info: set_instance_parameter_value acl_internal_snoop inMaxChannel 0 2018.03.23.10:02:26 Info: set_instance_parameter_value acl_internal_snoop inChannelWidth 0 2018.03.23.10:02:26 Info: set_instance_parameter_value acl_internal_snoop inErrorWidth 0 2018.03.23.10:02:26 Info: set_instance_parameter_value acl_internal_snoop inErrorDescriptor 2018.03.23.10:02:26 Info: set_instance_parameter_value acl_internal_snoop inUseEmptyPort 0 2018.03.23.10:02:26 Info: set_instance_parameter_value acl_internal_snoop inUseValid 1 2018.03.23.10:02:26 Info: set_instance_parameter_value acl_internal_snoop inUseReady 1 2018.03.23.10:02:26 Info: set_instance_parameter_value acl_internal_snoop inReadyLatency 0 2018.03.23.10:02:26 Info: set_instance_parameter_value acl_internal_snoop outDataWidth 33 2018.03.23.10:02:26 Info: set_instance_parameter_value acl_internal_snoop outMaxChannel 0 2018.03.23.10:02:26 Info: set_instance_parameter_value acl_internal_snoop outChannelWidth 0 2018.03.23.10:02:26 Info: set_instance_parameter_value acl_internal_snoop outErrorWidth 0 2018.03.23.10:02:26 Info: set_instance_parameter_value acl_internal_snoop outErrorDescriptor 2018.03.23.10:02:26 Info: set_instance_parameter_value acl_internal_snoop outUseEmptyPort 0 2018.03.23.10:02:26 Info: set_instance_parameter_value acl_internal_snoop outUseValid 1 2018.03.23.10:02:26 Info: set_instance_parameter_value acl_internal_snoop outUseReady 1 2018.03.23.10:02:26 Info: set_instance_parameter_value acl_internal_snoop outReadyLatency 0 2018.03.23.10:02:26 Info: add_connection clk_snoop.out_clk acl_internal_snoop.in_clk_0 2018.03.23.10:02:26 Info: add_connection reset.out_reset acl_internal_snoop.in_rst_0 2018.03.23.10:02:26 Info: add_interface cc_snoop avalon_streaming sink 2018.03.23.10:02:26 Info: set_interface_property cc_snoop EXPORT_OF acl_internal_snoop.in_0 2018.03.23.10:02:26 Info: add_instance sys_description_rom acl_rom_module 2018.03.23.10:02:26 Info: set_instance_parameter_value sys_description_rom INIT_FILE sys_description.hex 2018.03.23.10:02:26 Info: set_instance_parameter_value sys_description_rom ADDRESS_WIDTH 4 2018.03.23.10:02:26 Warning: add_connection: Extra arguments ignored clock 2018.03.23.10:02:26 Info: add_connection clk_1x.out_clk sys_description_rom.clk0 2018.03.23.10:02:26 Warning: add_connection: Extra arguments ignored reset 2018.03.23.10:02:26 Info: add_connection reset.out_reset sys_description_rom.reset0 2018.03.23.10:02:26 Info: set_instance_parameter_value sys_description_rom DATA_WIDTH 64 2018.03.23.10:02:26 Warning: add_connection: Extra arguments ignored avalon 2018.03.23.10:02:26 Info: add_connection cra_ring_rom.cra_master sys_description_rom.s0 2018.03.23.10:02:26 Info: set_instance_parameter_value sys_description_rom ADDRESS_WIDTH 5 2018.03.23.10:02:26 Info: set_instance_parameter_value cra_ring_rom ROM_W 5 2018.03.23.10:02:26 Info: set_instance_parameter_value cra_ring_rom ROM_EXT_W 0 2018.03.23.10:02:26 Info: set_instance_parameter_value cra_root ROM_EXT_W 0 2018.03.23.10:02:26 Info: save_system kernel_system.qsys 2018.03.23.10:02:26 Info: Replacing kernel_system.clk_1x with generic component 2018.03.23.10:02:26 Error: save_system kernel_system.qsys: 0