Changeset 1007


Ignore:
Timestamp:
Jul 16, 2015, 3:17:49 PM (9 years ago)
Author:
cfuguet
Message:

reconf: update the reconfiguration/tsar_generic_iob to comply with new
constructor parameters of the NIC and CHBUF_DMA peripherals.

Location:
branches/reconfiguration/platforms/tsar_generic_iob
Files:
3 edited

Legend:

Unmodified
Added
Removed

  • branches/reconfiguration/platforms/tsar_generic_iob/Makefile

    r1001 r1007  
    1 TAGS := cscope.out
     1RM             := rm -f
     2SOCLIB_CC      := soclib-cc
    23SOCLIB_CC_MODE := -m release
    34SOCLIB_CC_ARGS := $(SOCLIB_CC_MODE)
    … …  
    89#SOCLIB_CC_ARGS += -bcaba:vci_block_device_tsar
    910
    10 all: simul.x
     11TAGS           := cscope.out
     12TARGET         := simul.x
     13
     14objs           := $(wildcard *.o)
     15objs           += $(wildcard term[0-9])
     16objs           += $(wildcard $(TARGET))
     17objs           := $(strip $(objs))
     18
     19extra_objs     := $(wildcard scripts/*.pyc)
     20extra_objs     += $(wildcard hard_config.h)
     21extra_objs     += $(wildcard $(TAGS))
     22extra_objs     := $(strip $(extra_objs))
     23
     24all: $(TARGET)
    1125tags: $(TAGS)
    1226
    13 simul.x: top.cpp top.desc
    14         soclib-cc $(SOCLIB_CC_ARGS) -P -p top.desc -I. -o simul.x
     27.PHONY: $(TARGET)
     28$(TARGET): top.desc top.cpp
     29        $(SOCLIB_CC) $(SOCLIB_CC_ARGS) -P -p $< -I. -o $@
    1530
     31.PHONY: $(TAGS)
    1632$(TAGS): top.desc
    17         soclib-cc -p $< --tags --tags-type=cscope --tags-output=$@
     33        $(SOCLIB_CC) -p $< --tags --tags-type=cscope --tags-output=$@
    1834
     35.PHONY: clean
    1936clean:
    20         soclib-cc $(SOCLIB_CC_MODE) -x -p top.desc -I.
    21         rm -rf *.o *.x tty* term*
     37        $(SOCLIB_CC) $(SOCLIB_CC_MODE) -x -p top.desc -I.
     38ifneq ($(objs),)
     39        $(RM) $(objs)
     40endif
    2241
     42.PHONY: distclean
    2343distclean: clean
    24         rm -f $(TAGS) hard_config.h
    25         find . -name "*.pyc" -exec rm -f {} \;
    26 
    27 .PHONY: simul.x $(TAGS)
    28 
     44ifneq ($(extra_objs),)
     45        $(RM) $(extra_objs)
     46endif

  • branches/reconfiguration/platforms/tsar_generic_iob/scripts/arch.py

    r1000 r1007  
    287287            mapping.addGlobal('seg_kernel_code', kcode_vbase, kcode_size,
    288288                              'CXW_', vtype='ELF', x=x, y=y, pseg='RAM',
    289                               binpath='build/kernel/kernel.elf',
     289                              binpath='bin/kernel/kernel.elf',
    290290                              local=True, big=True)
    291291
    292292            mapping.addGlobal('seg_kernel_init', kinit_vbase, kinit_size,
    293293                              'CXW_', vtype='ELF', x=x, y=y, pseg='RAM',
    294                               binpath='build/kernel/kernel.elf',
     294                              binpath='bin/kernel/kernel.elf',
    295295                              local=True, big=True)
    296296
    … …  
    311311    mapping.addGlobal('seg_kernel_data', kdata_vbase, kdata_size,
    312312                      'CXW_', vtype='ELF', x=0, y=0, pseg='RAM',
    313                       binpath='build/kernel/kernel.elf', local=False,
     313                      binpath='bin/kernel/kernel.elf', local=False,
    314314                      big=True)
    315315
    316316    mapping.addGlobal('seg_kernel_uncdata', kuncdata_vbase, kuncdata_size,
    317317                      'CXW_', vtype='ELF', x=0, y=0, pseg='RAM',
    318                       binpath='build/kernel/kernel.elf', local=False,
     318                      binpath='bin/kernel/kernel.elf', local=False,
    319319                      big=True)
    320320

  • branches/reconfiguration/platforms/tsar_generic_iob/top.cpp

    r1001 r1007  
    151151#define almos_archinfo_pathname   "arch-info.bin@0xBFC08000:D"
    152152
    153 ///////////////////////////////////////////////////
     153///////////////////////////////////////////////////////////
    154154//               Parallelisation
    155 ///////////////////////////////////////////////////
    156 #define USE_OPENMP _OPENMP
    157 
    158 #if USE_OPENMP
     155//
     156// The _OPENMP flag is defined automatically by the
     157// compilation environment when compiling with the OpenMP
     158// support
     159///////////////////////////////////////////////////////////
     160#if _OPENMP
    159161#include <omp.h>
    160162#endif
    … …  
    512514   std::cout << std::endl;
    513515
    514 #if USE_OPENMP
     516#if _OPENMP
    515517   omp_set_dynamic(false);
    516518   omp_set_num_threads(threads_nr);
    … …  
    990992                                          maptab_iox,
    991993                                          NB_NIC_CHANNELS,
    992                                           0,                // mac_4 address
    993                                           0,                // mac_2 address
    994                                           nicMode );
     994                                          0,           // mac_4 address
     995                                          0,           // mac_2 address
     996                                          nicMode,
     997                                          12 );        // Inter Frame Gap
    995998
    996999   // Chained Buffer DMA controller
    … …  
    10011004                                          IntTab(0, IOX_CDMA_TGT_ID),
    10021005                                          64,          // burst size (bytes)
    1003                                           2*NB_NIC_CHANNELS );
     1006                                          NB_CMA_CHANNELS,
     1007                                          4 );         // # pipelined burst
    10041008#else
    10051009   VciTargetError<vci_param_ext> merror_nic( "merror_nic",
    … …  
    10771081   TsarCluster* clusters[X_SIZE][Y_SIZE];
    10781082
    1079 #if USE_OPENMP
     1083#if _OPENMP
    10801084#pragma omp parallel
    10811085    {
    … …  
    10871091            size_t y = i % Y_SIZE;
    10881092
    1089 #if USE_OPENMP
     1093#if _OPENMP
    10901094#pragma omp critical
    10911095            {
    … …  
    11701174            );
    11711175
    1172 #if USE_OPENMP
     1176#if _OPENMP
    11731177            } // end critical
    11741178#endif
    11751179        } // end for
    1176 #if USE_OPENMP
     1180#if _OPENMP
    11771181    }
    11781182#endif
Note: See TracChangeset for help on using the changeset viewer.