|  | # Copyright (C) 2017-2020  The Project X-Ray Authors | 
|  | # | 
|  | # Use of this source code is governed by a ISC-style | 
|  | # license that can be found in the LICENSE file or at | 
|  | # https://opensource.org/licenses/ISC | 
|  | # | 
|  | # SPDX-License-Identifier: ISC | 
|  | source "$::env(XRAY_DIR)/utils/utils.tcl" | 
|  |  | 
|  | create_project -force -part $::env(XRAY_PART) design design | 
|  |  | 
|  | read_verilog $::env(FUZDIR)/top.v | 
|  | synth_design -top top | 
|  |  | 
|  | set_property -dict "PACKAGE_PIN $::env(XRAY_PIN_00) IOSTANDARD LVCMOS33" [get_ports i] | 
|  | set_property -dict "PACKAGE_PIN $::env(XRAY_PIN_01) IOSTANDARD LVCMOS33" [get_ports o] | 
|  |  | 
|  | create_pblock roi | 
|  | resize_pblock [get_pblocks roi] -add "$::env(XRAY_ROI)" | 
|  |  | 
|  | set_property CFGBVS VCCO [current_design] | 
|  | set_property CONFIG_VOLTAGE 3.3 [current_design] | 
|  | set_property BITSTREAM.GENERAL.PERFRAMECRC YES [current_design] | 
|  | set_param tcl.collectionResultDisplayLimit 0 | 
|  |  | 
|  | place_design | 
|  | route_design | 
|  |  | 
|  | # write_checkpoint -force design.dcp | 
|  |  | 
|  | set fp [open "../todo.txt" r] | 
|  | set todo_lines {} | 
|  | for {gets $fp line} {$line != ""} {gets $fp line} { | 
|  | lappend todo_lines [split $line .] | 
|  | } | 
|  | close $fp | 
|  |  | 
|  | # each run can fail up to three times so we need to prepare 3*todo_lines tiles to work on | 
|  | set tiles [expr 3 * [llength $todo_lines]] | 
|  |  | 
|  | set int_l_tiles [randsample_list $tiles [filter [pblock_tiles roi] {TYPE == INT_L}]] | 
|  | set int_r_tiles [randsample_list $tiles [filter [pblock_tiles roi] {TYPE == INT_R}]] | 
|  |  | 
|  |  | 
|  | for {set idx 0} {$idx < [llength $todo_lines]} {incr idx} { | 
|  | set line [lindex $todo_lines $idx] | 
|  | puts "== $idx: $line" | 
|  |  | 
|  | set tile_type [lindex $line 0] | 
|  | set dst_wire [lindex $line 1] | 
|  | set src_wire [lindex $line 2] | 
|  |  | 
|  | set mynet [create_net mynet_$idx] | 
|  | set mylut [create_cell -reference LUT1 mylut_$idx] | 
|  |  | 
|  | if {$src_wire == "VCC_WIRE"} { | 
|  | set mytie [create_cell -reference VCC mytie_$idx] | 
|  | connect_net -net $mynet -objects "$mytie/P $mylut/I0" | 
|  | } | 
|  |  | 
|  | if {$src_wire == "GND_WIRE"} { | 
|  | set mytie [create_cell -reference GND mytie_$idx] | 
|  | connect_net -net $mynet -objects "$mytie/G $mylut/I0" | 
|  | } | 
|  |  | 
|  | set tries 0 | 
|  | while {1} { | 
|  | set tile_idx [expr $tries + [expr $idx * 3]] | 
|  | incr tries | 
|  |  | 
|  | if {$tile_type == "INT_L"} {set tile [lindex $int_l_tiles $tile_idx]; set other_tile [lindex $int_r_tiles $tile_idx]} | 
|  | if {$tile_type == "INT_R"} {set tile [lindex $int_r_tiles $tile_idx]; set other_tile [lindex $int_l_tiles $tile_idx]} | 
|  |  | 
|  | set recv_site [get_sites -of_objects [get_site_pins -of_objects [get_nodes -downhill \ | 
|  | -of_objects [get_nodes -of_objects [get_wires $other_tile/CLK*0]]]]] | 
|  |  | 
|  | set_property -dict "LOC $recv_site BEL A6LUT" $mylut | 
|  |  | 
|  | set rc [route_via $mynet "$tile/$src_wire $tile/$dst_wire" 0] | 
|  | if {$rc != 0} { | 
|  | puts "ROUTING DONE!" | 
|  | break | 
|  | } | 
|  |  | 
|  | # fallback | 
|  | puts "WARNING: failed to route net" | 
|  | write_checkpoint -force route_todo_$idx.$tries.fail.dcp | 
|  |  | 
|  | puts "Rolling back route" | 
|  | set_property is_route_fixed 0 $mynet | 
|  | set_property is_bel_fixed 0 $mylut | 
|  | set_property is_loc_fixed 1 $mylut | 
|  | route_design -unroute -nets $mynet | 
|  |  | 
|  | # sometimes it gets stuck in specific src -> dst locations | 
|  | if {$tries >= 3} { | 
|  | error "ERROR: failed to route net after $tries tries" | 
|  | } | 
|  | } | 
|  | } | 
|  |  | 
|  | route_design | 
|  | write_checkpoint -force design.dcp | 
|  | write_bitstream -force design.bit | 
|  | write_pip_txtdata design.txt |