Skip to content

Commit 2195ebc

Browse files
TopiLeppanenTopiLeppanen
committed
AlmaIF: add tests for auto generated tb
Also tests the functionality of intel bram-models. (Doesn't test that they infer correctly)
1 parent 3f0f8ac commit 2195ebc

File tree

7 files changed

+266
-1
lines changed

7 files changed

+266
-1
lines changed

‎openasip/data/ProGe/tb/almaif/almaif-tb.vhdl.tmpl‎

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -560,7 +560,7 @@ begin
560560
file_open(dmem_dump_file, dmem_dump_path, write_mode);
561561
for i in 0 to dmem_size/4-1 loop
562562
axi_read(dmem_start+i*4, dmem_word);
563-
write(line_out, integer'image(to_integer(unsigned(dmem_word))));
563+
write(line_out, integer'image(to_integer(signed(dmem_word))));
564564
writeline(dmem_dump_file, line_out);
565565
end loop;
566566
file_close(dmem_dump_file);

‎testsuite/systemtest_long/procgen/PlatformIntegrator/AlmaIFIntegrator/result_templates/default_data_tb.txt‎

Lines changed: 64 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -0,0 +1,64 @@
1+
0
2+
1
3+
1
4+
2
5+
3
6+
5
7+
8
8+
13
9+
21
10+
34
11+
55
12+
89
13+
144
14+
233
15+
377
16+
610
17+
987
18+
1597
19+
2584
20+
4181
21+
6765
22+
10946
23+
17711
24+
28657
25+
46368
26+
75025
27+
121393
28+
196418
29+
317811
30+
514229
31+
832040
32+
1346269
33+
2178309
34+
3524578
35+
5702887
36+
9227465
37+
14930352
38+
24157817
39+
39088169
40+
63245986
41+
102334155
42+
165580141
43+
267914296
44+
433494437
45+
701408733
46+
1134903170
47+
1836311903
48+
-1323752223
49+
512559680
50+
-811192543
51+
-298632863
52+
-1109825406
53+
-1408458269
54+
1776683621
55+
368225352
56+
2144908973
57+
-1781832971
58+
363076002
59+
-1418756969
60+
-1055680967
61+
1820529360
62+
764848393
63+
-1709589543
64+
-944741150

‎testsuite/systemtest_long/procgen/PlatformIntegrator/AlmaIFIntegrator/result_templates/default_header_tb.txt‎

Lines changed: 10 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -0,0 +1,10 @@
1+
DMEM size: 2048
2+
CQMEM size: 32768
3+
IMEM start: 32768
4+
DMEM start: 98304
5+
CQMEM start: 65536
6+
IMEM Initialization complete
7+
DMEM Initialization complete
8+
CQMEM Initialization complete
9+
Core done
10+
Output written

‎testsuite/systemtest_long/procgen/PlatformIntegrator/AlmaIFIntegrator/src/fib_tb.c‎

Lines changed: 55 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -0,0 +1,55 @@
1+
#define __global__ __attribute__((address_space(5)))
2+
#define __param__ __attribute__((address_space(6)))
3+
#define __private__ __attribute__((address_space(0)))
4+
#include "tceops.h"
5+
6+
#define N 64
7+
8+
volatile __param__ int done = 0;
9+
10+
__param__ char test[4]={1,2,3,4};
11+
12+
volatile __param__ int results[N];
13+
14+
15+
int fib(int n)
16+
{
17+
volatile int a1=0, a2=1, retval;
18+
if (n <= 1)
19+
return n;
20+
for (volatile int i=0; i<n-1; ++i)
21+
{
22+
retval = a1+a2;
23+
a1 = a2;
24+
a2 = retval;
25+
}
26+
return retval;
27+
}
28+
29+
int
30+
main(void)
31+
{
32+
// Force memory accesses with volatile
33+
for(volatile int i=0; i<N; ++i)
34+
{
35+
volatile int val = fib(i);
36+
volatile char* val_c = (volatile char*)(&val);
37+
volatile short* val_h = (volatile short*)(&val);
38+
volatile char temp8;
39+
volatile short temp16;
40+
// Do some byte juggling to test 16- and 8-bit accesses
41+
temp8 = val_c[2];
42+
val_c[2] = val_c[0];
43+
val_c[0] = temp8;
44+
temp8 = val_c[3];
45+
val_c[3] = val_c[1];
46+
val_c[1] = temp8;
47+
temp16 = val_h[1];
48+
val_h[1] = val_h[0];
49+
val_h[0] = temp16;
50+
51+
results[i] = val;
52+
}
53+
done = 1;
54+
return 0;
55+
}

‎testsuite/systemtest_long/procgen/PlatformIntegrator/AlmaIFIntegrator/tcetest_almaif_tb.sh‎

Lines changed: 118 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -0,0 +1,118 @@
1+
#!/bin/bash
2+
### TCE TESTCASE
3+
### title: Generate a processor with AlmaIFIntegrator and integrated testbench
4+
5+
TPEF=prog.tpef
6+
PROGE_OUT=proge-out
7+
ENT=almaif_core
8+
INTEG=AlmaIFIntegrator
9+
10+
DMEM_DUMP=dmem_raw.log
11+
DMEM_STRIPPED=dmem_stripped.log
12+
13+
TEST_NAMES=(basic_tb intel)
14+
15+
while getopts "dvst:" OPTION
16+
do
17+
case $OPTION in
18+
d)
19+
leavedirty=true
20+
;;
21+
v)
22+
verbose=true
23+
;;
24+
s)
25+
spam=true
26+
;;
27+
t)
28+
one_test=true
29+
testcase=$OPTARG
30+
;;
31+
?)
32+
exit 1
33+
;;
34+
esac
35+
done
36+
37+
function eexit {
38+
echo $1
39+
if [ -f compile.log ]; then cat compile.log; fi
40+
if [ -f sim.log ]; then cat sim.log; fi
41+
exit 1
42+
}
43+
44+
function clear_test_data {
45+
rm -f *.img
46+
rm -rf $PROGE_OUT
47+
rm -f *.tpef
48+
rm -f prog_imem_pkg.vhdl
49+
rm -f run.log
50+
rm -f $DMEM_DUMP
51+
rm -f $DMEM_STRIPPED
52+
}
53+
54+
function run_test {
55+
NAME=$1
56+
source test_definitions/$NAME.sh
57+
58+
clear_test_data
59+
60+
if [ "${spam}" == "true" ]; then
61+
V_SWITCH=-v
62+
fi
63+
64+
tcecc -O3 -a $ADF -o $TPEF $SRC || eexit "tcecc failed with $SRC"
65+
generateprocessor -t -o $PROGE_OUT -g $INTEG -d $DMEM -f $IMEM -e $ENT \
66+
-p $TPEF --hdb-list=$HDBS --icd-arg-list=$ICD_ARGS \
67+
$EXTRA_OPT $V_SWITCH $ADF || eexit "ProGe failed with $NAME"
68+
generatebits -w 4 -d -e $ENT -x $PROGE_OUT -p $TPEF $EXTRA_PIG_OPTS $ADF \
69+
|| eexit "generatebits failed with $NAME"
70+
71+
COMPLETION_SIGNAL_ADDR=$(echo "mach $ADF;prog $TPEF;symbol_address done" |\
72+
ttasim | head -n1)
73+
74+
75+
# If GHDL is found from PATH, compile and simulate
76+
GHDL=$(which ghdl 2> /dev/null)
77+
if [ "x${GHDL}" != "x" ]
78+
then
79+
cd $PROGE_OUT || eexit "No such dir: $PROGE_OUT"
80+
81+
bash ghdl_compile.sh -v93c -a
82+
bash ghdl_platform_compile.sh -v93c
83+
bash ghdl_simulate.sh -v93c -r 10000000000 -n tta_almaif_tb \
84+
-g "imem_image=../prog.img" \
85+
-g "dmem_image=../prog_param.img" \
86+
-g "completion_signal_address_g=${COMPLETION_SIGNAL_ADDR}" \
87+
-g "log_path=../run.log" \
88+
-g "dmem_dump_path=../${DMEM_DUMP}"
89+
cd ..
90+
91+
OUTPUT_BUFFER_ADDR=$(echo "mach $ADF;prog $TPEF;symbol_address results" |\
92+
ttasim | head -n1)
93+
OUTPUT_BUFFER_IDX=$((OUTPUT_BUFFER_ADDR/4))
94+
95+
cat ${DMEM_DUMP} | head -n$((OUTPUT_BUFFER_IDX+64)) | tail -n 64 > $DMEM_STRIPPED
96+
97+
diff run.log $HEADER || eexit "Output header didn't match for $NAME"
98+
diff $DMEM_STRIPPED $DATA || eexit "Output data didn't match for $NAME"
99+
fi
100+
101+
if [ "${verbose}" == "true" ]; then
102+
echo "$NAME PASSED!"
103+
fi
104+
}
105+
106+
if [ "${one_test}" == "true" ]; then
107+
run_test $testcase
108+
else
109+
for test in "${TEST_NAMES[@]}"; do
110+
run_test $test
111+
done
112+
fi
113+
114+
115+
if [ "${leavedirty}" != "true" ]; then
116+
clear_test_data
117+
fi
118+

‎testsuite/systemtest_long/procgen/PlatformIntegrator/AlmaIFIntegrator/test_definitions/basic_tb.sh‎

Lines changed: 9 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -0,0 +1,9 @@
1+
ADF="mach/mach.adf"
2+
ICD_ARGS="debugger:external"
3+
DMEM="onchip"
4+
IMEM="onchip"
5+
SRC="src/fib_tb.c"
6+
HEADER="result_templates/default_header_tb.txt"
7+
DATA="result_templates/default_data_tb.txt"
8+
EXTRA_OPTS=""
9+
HDBS="generate_base32.hdb,generate_lsu_32.hdb,generate_rf_iu.hdb"

‎testsuite/systemtest_long/procgen/PlatformIntegrator/AlmaIFIntegrator/test_definitions/intel.sh‎

Lines changed: 9 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -0,0 +1,9 @@
1+
ADF="mach/mach.adf"
2+
ICD_ARGS="debugger:external,bram-vendor:intel"
3+
DMEM="onchip"
4+
IMEM="onchip"
5+
SRC="src/fib_tb.c"
6+
HEADER="result_templates/default_header_tb.txt"
7+
DATA="result_templates/default_data_tb.txt"
8+
EXTRA_OPTS=""
9+
HDBS="generate_base32.hdb,generate_lsu_32.hdb,generate_rf_iu.hdb"

0 commit comments

Comments
 (0)