Ignore:
Timestamp:
Nov 29, 2012, 1:21:07 PM (12 years ago)
Author:
bouyer
Message:

This VHDL implementation uses rings, use rings here too.

Location:
trunk/platforms/platform_fpga_de2-115
Files:
2 edited

Legend:

Unmodified
Added
Removed
  • trunk/platforms/platform_fpga_de2-115/platform_desc

    r274 r275  
    1212        Uses('caba:vci_simhelper'),
    1313        Uses('caba:vci_framebuffer'),
    14         Uses('caba:vci_vgmn'),
     14        Uses('caba:vci_simple_ring_fast',
     15              ring_cmd_data_size=40,
     16              ring_rsp_data_size=33
     17        ),
    1518        Uses('caba:vci_logger'),
    1619        Uses('caba:vci_mem_cache_v4'),
  • trunk/platforms/platform_fpga_de2-115/top.cpp

    r274 r275  
    1818#include "vci_simple_ram.h"
    1919#include "vci_multi_tty.h"
    20 #include "vci_vgmn.h"
     20#include "vci_simple_ring_fast.h"
    2121#include "vci_mem_cache_v4.h"
    2222#include "vci_cc_vcache_wrapper_v4.h"
     
    222222        soclib::caba::VciBlockDeviceTsarV4<vci_param> *vcibd;
    223223        soclib::caba::VciCcVCacheWrapperV4<vci_param, proc_iss > *proc3;
    224         soclib::caba::VciVgmn<vci_param> *ringp;
    225         soclib::caba::VciVgmn<vci_param> *ringc;
     224        soclib::caba::VciSimpleRingFast<vci_param, 40, 33> *ringp;
     225        soclib::caba::VciSimpleRingFast<vci_param, 40, 33> *ringc;
    226226#pragma omp parallel sections
    227227  {
     
    277277        signal_proc2_it4 = new sc_signal<bool>("mips2_it4");
    278278        signal_proc2_it5 = new sc_signal<bool>("mips2_it5");
    279         ringp = new soclib::caba::VciVgmn<vci_param>
    280           ("ringp",maptabp, 5, 7, /*3*/1, 8);
     279        ringp = new soclib::caba::VciSimpleRingFast<vci_param, 40, 33>
     280          ("ringp",maptabp, IntTab(), 4, 5, 7);
    281281        vcixicu = new soclib::caba::VciXicu<vci_param>
    282282          ("vcixicu", maptabp, IntTab(4), 4 /* npti */, 2 /* nhwi */, 4 /* nwti */, 12 /* nirq */);
     
    305305          ("memc",maptabp,maptabc,maptabx,IntTab(0),IntTab(4),IntTab(0), IntTab(4),16,256,16, 1024, 4, 4, DEBUG_CYCLE, true);
    306306        signal_vci_ixr_memc = new soclib::caba::VciSignals<vci_param>("vci_ixr_memc");
    307         ringc = new soclib::caba::VciVgmn<vci_param>
    308           ("ringc",maptabc, 5, 5, /*2*/1, 8);
     307        ringc = new soclib::caba::VciSimpleRingFast<vci_param, 40, 33>
     308          ("ringc",maptabc, IntTab(), 4, 5, 5);
    309309#ifdef VCI_LOGGER_ON_L1
    310310        soclib::caba::VciLogger<vci_param> vci_logger0("vci_logger0",maptabp);
Note: See TracChangeset for help on using the changeset viewer.