static void show(BOOL force)
{ /* output display */
if (force || strcmp(oldstat,status)!=0)
{
if (mip->ERNUM) aprint(BLINKING,2,2,status);
else aprint(STATCOL,2,2,status);
strcpy(oldstat,status);
}
aprint(BOLD,dbeg,3,display);
}
static void drawit(void)
{ /* Draw calculator */
int i,j;
char line[40],tline[40],bline[40];
cset(1);
line[0]=DTLHC;
for (i=1;i<38;i++) line[i]=DHORZ;
line[38]=DTRHC;
line[39]='\0';
aprint(ORDINARY,1,1,line);
for (i=1;i<22;i++) apchar(ORDINARY,1,1+i,DVERT);
line[0]=DBLHC;
line[38]=DBRHC;
aprint(ORDINARY,1,23,line);
for (i=1;i<22;i++) apchar(ORDINARY,39,1+i,DVERT);
line[0]=LSIDE; /* draw in the bar */
for (i=1;i<38;i++) line[i]=HORZ;
line[38]=RSIDE;
aprint(ORDINARY,1,4,line);
line[0]=tline[0]=bline[0]=SPACE;
line[36]=tline[36]=bline[36]=SPACE;
line[37]=tline[37]=bline[37]='\0';
for (i=1;i<36;i++)
{
switch (i%5)
{
case 1 : tline[i]=TLHC;
bline[i]=BLHC;
line[i]=VERT;
break;
default: tline[i]=HORZ;
bline[i]=HORZ;
line[i]=SPACE;
break;
case 0 : tline[i]=TRHC;
bline[i]=BRHC;
line[i]=VERT;
break;
}
}
for (j=0;j<6;j++)
{
aprint(ORDINARY,2,5+3*j,tline);
aprint(ORDINARY,2,6+3*j,line);
aprint(ORDINARY,2,7+3*j,bline);
}
cset(0);
for (j=0;j<6;j++)
for (i=0;i<7;i++)
aprint(ORDINARY,4+5*i,6+3*j,keys[j][i]);
aprint(HELPCOL,2,24,"Type 'H' for help on/off, 'O' to exit");
cotstr(x,mip->IOBUFF);
just((char *)mip->IOBUFF);
getstat();
show(TRUE);
}
int main()
{ /* MIRACL rational calculator */
int i,j,k,p,q,c,hpos;
BOOL over,help;
screen();
#if MIRACL==16
mip=mirsys(10,0); /*** 16-bit computer ***/
#else
mip=mirsys(6,0); /*** 32-bit computer ***/
#endif
mip->ERCON=TRUE;
x=mirvar(0);
for (i=0;i<=top;i++) y[i]=mirvar(0);
m=mirvar(0);
t=mirvar(0);
radeg=mirvar(0);
loge2=mirvar(0);
loge10=mirvar(0);
eps=mirvar(0);
mip->pi=mirvar(0);
cinstr(mip->pi,cpi); /* read in constants */
fpmul(mip->pi,1,180,radeg);
cinstr(loge2,clg2);
cinstr(loge10,clg10);
cinstr(eps,ceps);
help=OFF;
show(TRUE);
p=6;
q=0;
flag=OFF;
newx=OFF;
over=FALSE;
setopts();
clrall();
drawit();
while (!over)
{ /* main loop */
if (mip->ERNUM)
{
aprint(ORDINARY,4+5*p,6+3*q,keys[q][p]);
p=5,q=0;
}
if (width==80 || !help)
{
aprint(INVER,4+5*p,6+3*q,keys[q][p]);
curser(1,24);
c=gethit();
aprint(ORDINARY,4+5*p,6+3*q,keys[q][p]);
}
else while ((c=gethit())!='H') ;
result=TRUE;
if ((k=arrow(c))!=0)
{ /* arrow key hit */
if (k==1 && q>0) q--;
if (k==2 && q<5) q++;
if (k==3 && p<6) p++;
if (k==4 && p>0) p--;
continue;
}
if (c=='H')
{ /* switch help on/off */
help=!help;
for (i=1;i<=24;i++)
{
if (width==80) hpos=41;
else hpos=1;
if (help) aprint(HELPCOL,hpos,i,htext[i-1]);
else lclr(hpos,i);
}
if (width==40 && !help) drawit();
continue;
}
if (c>='A' && c<='F')
{ /* hex only */
if (!next(c)) putchar(BELL);
else show(FALSE);
continue;
}
for (j=0;j<6;j++)
for (i=0;i<7;i++)
if (c==qkeys[j][i]) p=i,q=j,c=' ';
if (c==8 || c==127) p=6,q=1,c=' '; /* aliases */
if (c==',' || c=='a') p=5,q=5,c=' ';
if (c=='O' || c==ESC) p=6,q=0,c=' ';
if (c==13) p=6,q=5,c=' ';
if (c=='[' || c=='{') p=3,q=5,c=' ';
if (c==']' || c=='}') p=4,q=5,c=' ';
if (c=='d') p=5,q=2,c=' ';
if (c=='b') p=5,q=3,c=' ';
if (c=='^') p=3,q=2,c=' ';
if (c==' ') over=act(p,q);
else continue;
absol(x,t);
if (fcomp(t,eps)<0) zero(x);
if (result)
{ /* output result to display */
cotstr(x,mip->IOBUFF);
just((char *)mip->IOBUFF);
if (mip->ERNUM<0)
{ /* convert to radix and try again */
mip->ERNUM=0;
mip->RPOINT=ON;
cotstr(x,mip->IOBUFF);
putchar(BELL);
just((char *)mip->IOBUFF);
}
clr();
}
if (newx)
{ /* update display */
getstat();
show(FALSE);
}
}
curser(1,24);
restore();
return 0;
}
static BOOL act(int p,int q)
{ /* act on selected key */
int k,n,c;
aprint(PRESSED,4+5*p,6+3*q,keys[q][p]);
switch(p+7*q)
{
case 0: if (degrees) fmul(x,radeg,x);
if (hyp) fsinh(x,x);
else fsin(x,x);
newx=TRUE;
break;
case 1: if (degrees) fmul(x,radeg,x);
if (hyp) fcosh(x,x);
else fcos(x,x);
newx=TRUE;
break;
case 2: if (degrees) fmul(x,radeg,x);
if (hyp) ftanh(x,x);
else ftan(x,x);
newx=TRUE;
break;
case 3: if (lgbase>0)
{
n=size(x);
if (abs(n)<MR_TOOBIG)
{
convert(lgbase,x);
if (n<0) frecip(x,x);
fpower(x,abs(n),x);
newx=TRUE;
break;
}
if (lgbase==2) fmul(x,loge2,x);
if (lgbase==10) fmul(x,loge10,x);
}
fexp(x,x);
newx=TRUE;
break;
case 4: mip->RPOINT=!mip->RPOINT;
newx=TRUE;
break;
case 5: clrall();
newx=TRUE;
break;
case 6: return TRUE;
case 7: if (hyp) fasinh(x,x);
else fasin(x,x);
if (degrees) fdiv(x,radeg,x);
newx=TRUE;
break;
case 8: if (hyp) facosh(x,x);
else facos(x,x);
if (degrees) fdiv(x,radeg,x);
newx=TRUE;
break;
case 9: if (hyp) fatanh(x,x);
else fatan(x,x);
if (degrees) fdiv(x,radeg,x);
newx=TRUE;
break;
case 10: flog(x,x);
if (lgbase==2) fdiv(x,loge2,x);
if (lgbase==10) fdiv(x,loge10,x);
newx=TRUE;
break;
case 11: newx=TRUE;
k=3;
forever
{
aprint(INVER,2+stptr[k],2,settings[k][option[k]]);
curser(2+stptr[k],2);
c=arrow(gethit());
if (c==1)
{
if (option[k]==nops[k]) option[k]=0;
else option[k]+=1;
continue;
}
aprint(STATCOL,2+stptr[k],2,settings[k][option[k]]);
if (c==0 || c==2) break;
if (c==4 && k>0) k--;
if (c==3 && k<3) k++;
}
setopts();
break;
case 12: chekit(7);
break;
case 13: result=FALSE;
if (ipt==0) break;
ipt--;
mybuff[ipt]='\0';
if (ipt==0) clr();
just(mybuff);
cinstr(x,mybuff);
newx=TRUE;
break;
case 14: if (!next('7')) putchar(BELL);
break;
case 15: if (!next('8')) putchar(BELL);
break;
case 16: if (!next('9')) putchar(BELL);
break;
case 17: chekit(6);
break;
case 18: chekit(5);
break;
case 19: chekit(4);
break;
case 20: copy(m,x);
newx=TRUE;
break;
case 21: if (!next('4')) putchar(BELL);
break;
case 22: if (!next('5')) putchar(BELL);
break;
case 23: if (!next('6')) putchar(BELL);
break;
case 24: fmul(x,x,x);
newx=TRUE;
break;
case 25: froot(x,2,x);
newx=TRUE;
break;
case 26: chekit(3);
break;
case 27: brkt=0;
chekit(0);
flag=OFF;
fadd(m,x,m);
newx=TRUE;
break;
case 28: if (!next('1')) putchar(BELL);
break;
case 29: if (!next('2')) putchar(BELL);
break;
case 30: if (!next('3')) putchar(BELL);
break;
case 31: frecip(x,x);
newx=TRUE;
break;
case 32: fpi(x);
newx=TRUE;
break;
case 33: chekit(2);
break;
case 34: negify(x,x);
newx=TRUE;
break;
case 35: if (!next('0')) putchar(BELL);
break;
case 36: if (!next('/')) putchar(BELL);
break;
case 37: if (!next('.')) putchar(BELL);
break;
case 38: if (ipt>0)
{
putchar(BELL);
result=FALSE;
}
else
{
zero(x);
brkt+=1;
newx=TRUE;
}
break;
case 39: if (brkt>0)
{
chekit(0);
brkt-=1;
}
else
{
putchar(BELL);
result=FALSE;
}
break;
case 40: chekit(1);
break;
case 41: brkt=0;
equals(0);
flag=OFF;
break;
}
return FALSE;
}
static void lclr(int x,int y)
{ /* clear from x,y to end of line */
aprint(BGROUND,x,y," ");
}
void get_config()
{
int flag = 0, sflag = 0, i, prt = 0;
int reprint_screen = 0;
ulong page;
#if NMOD_FRAMEBUFFER > 0
stop_record();
#endif
popup();
wait_keyup();
while(!flag) {
cprint(POP_Y+1, POP_X+2, "Configuration:");
cprint(POP_Y+3, POP_X+6, "(1) Test Selection");
cprint(POP_Y+4, POP_X+6, "(2) Address Range");
cprint(POP_Y+5, POP_X+6, "(3) Memory Sizing");
cprint(POP_Y+6, POP_X+6, "(4) Error Summary");
cprint(POP_Y+7, POP_X+6, "(5) Error Report Mode");
cprint(POP_Y+8, POP_X+6, "(6) ECC Mode");
cprint(POP_Y+9, POP_X+6, "(7) Restart");
cprint(POP_Y+10, POP_X+6, "(8) Refresh Screen");
cprint(POP_Y+11, POP_X+6, "(9) Adv. Options");
cprint(POP_Y+12,POP_X+6,"(0) Continue");
/* Wait for key release */
/* Fooey! This nuts'es up the serial input. */
sflag = 0;
switch(get_key()) {
case 2:
/* 1 - Test Selection */
popclear();
cprint(POP_Y+1, POP_X+2, "Test Selection:");
cprint(POP_Y+3, POP_X+6, "(1) Default Tests");
cprint(POP_Y+4, POP_X+6, "(2) Skip Current Test");
cprint(POP_Y+5, POP_X+6, "(3) Select Test");
cprint(POP_Y+6, POP_X+6, "(4) Select Bit Fade Test");
cprint(POP_Y+7, POP_X+6, "(0) Continue");
if (v->testsel < 0) {
cprint(POP_Y+3, POP_X+5, ">");
} else {
cprint(POP_Y+5, POP_X+5, ">");
}
wait_keyup();
while (!sflag) {
switch(get_key()) {
case 2:
/* Default */
if (v->testsel == 9) {
bail++;
}
v->testsel = -1;
find_ticks();
sflag++;
cprint(LINE_INFO, COL_TST, "Std");
break;
case 3:
/* Skip test */
bail++;
sflag++;
break;
case 4:
/* Select test */
popclear();
cprint(POP_Y+1, POP_X+3,
"Test Selection:");
cprint(POP_Y+4, POP_X+5,
"Test Number [0-9]: ");
i = getval(POP_Y+4, POP_X+24, 0);
if (i <= 9) {
if (i != v->testsel) {
v->pass = -1;
v->test = -1;
}
v->testsel = i;
}
find_ticks();
sflag++;
bail++;
cprint(LINE_INFO, COL_TST, "#");
dprint(LINE_INFO, COL_TST+1, i, 2, 1);
break;
case 5:
if (v->testsel != 9) {
v->pass = -1;
v->test = -1;
}
v->testsel = 9;
find_ticks();
sflag++;
bail++;
cprint(LINE_INFO, COL_TST, "#");
dprint(LINE_INFO, COL_TST+1, 9, 2, 1);
break;
case 11:
case 57:
sflag++;
break;
}
}
popclear();
break;
case 3:
/* 2 - Address Range */
popclear();
cprint(POP_Y+1, POP_X+2, "Test Address Range:");
cprint(POP_Y+3, POP_X+6, "(1) Set Lower Limit");
cprint(POP_Y+4, POP_X+6, "(2) Set Upper Limit");
cprint(POP_Y+5, POP_X+6, "(3) Test All Memory");
cprint(POP_Y+6, POP_X+6, "(0) Continue");
wait_keyup();
while (!sflag) {
switch(get_key()) {
case 2:
/* Lower Limit */
popclear();
cprint(POP_Y+2, POP_X+4,
"Lower Limit: ");
cprint(POP_Y+4, POP_X+4,
"Current: ");
aprint(POP_Y+4, POP_X+13, v->plim_lower);
cprint(POP_Y+6, POP_X+4,
"New: ");
page = getval(POP_Y+6, POP_X+9, 12);
if (page + 1 <= v->plim_upper) {
v->plim_lower = page;
bail++;
}
adj_mem();
find_ticks();
sflag++;
break;
case 3:
/* Upper Limit */
popclear();
cprint(POP_Y+2, POP_X+4,
"Upper Limit: ");
cprint(POP_Y+4, POP_X+4,
"Current: ");
aprint(POP_Y+4, POP_X+13, v->plim_upper);
cprint(POP_Y+6, POP_X+4,
"New: ");
page = getval(POP_Y+6, POP_X+9, 12);
if (page - 1 >= v->plim_lower) {
v->plim_upper = page;
bail++;
}
adj_mem();
find_ticks();
sflag++;
break;
case 4:
/* All of memory */
v->plim_lower = 0;
v->plim_upper = v->pmap[v->msegs - 1].end;
bail++;
adj_mem();
find_ticks();
sflag++;
break;
case 11:
case 57:
/* 0/CR - Continue */
sflag++;
break;
}
}
popclear();
break;
case 4:
/* 3 - Memory Sizing */
popclear();
cprint(POP_Y+1, POP_X+2, "Memory Sizing:");
cprint(POP_Y+3, POP_X+6, "(1) BIOS - Std");
if (e820_nr) {
cprint(POP_Y+4, POP_X+6, "(2) BIOS - All");
cprint(POP_Y+5, POP_X+6, "(3) Probe");
cprint(POP_Y+6, POP_X+6, "(0) Continue");
cprint(POP_Y+2+memsz_mode, POP_X+5, ">");
} else {
cprint(POP_Y+4, POP_X+6, "(3) Probe");
cprint(POP_Y+5, POP_X+6, "(0) Continue");
if (memsz_mode == SZ_MODE_BIOS) {
cprint(POP_Y+3, POP_X+5, ">");
} else {
cprint(POP_Y+4, POP_X+5, ">");
}
}
wait_keyup();
while (!sflag) {
switch(get_key()) {
case 2:
memsz_mode = SZ_MODE_BIOS;
wait_keyup();
restart();
/*
mem_size();
v->test = 0;
v->pass = 0;
v->total_ticks = 0;
bail++;
sflag++;
*/
break;
case 3:
memsz_mode = SZ_MODE_BIOS_RES;
wait_keyup();
restart();
/*
mem_size();
v->test = 0;
v->pass = 0;
v->total_ticks = 0;
bail++;
sflag++;
*/
break;
case 4:
memsz_mode = SZ_MODE_PROBE;
wait_keyup();
restart();
/*
mem_size();
v->test = 0;
v->pass = 0;
v->total_ticks = 0;
bail++;
sflag++;
*/
break;
case 11:
case 57:
/* 0/CR - Continue */
sflag++;
break;
}
}
popclear();
break;
case 5:
/* 4 - Show error summary */
popclear();
for (i=0; tseq[i].msg != NULL; i++) {
cprint(POP_Y+1+i, POP_X+2, "Test:");
dprint(POP_Y+1+i, POP_X+8, i, 2, 1);
cprint(POP_Y+1+i, POP_X+12, "Errors:");
dprint(POP_Y+1+i, POP_X+20, tseq[i].errors,
5, 1);
}
wait_keyup();
while (get_key() == 0);
popclear();
break;
case 6:
/* 5 - Printing Mode */
popclear();
cprint(POP_Y+1, POP_X+2, "Printing Mode:");
cprint(POP_Y+3, POP_X+6, "(1) Individual Errors");
cprint(POP_Y+4, POP_X+6, "(2) BadRAM Patterns");
cprint(POP_Y+5, POP_X+6, "(3) Error Counts Only");
cprint(POP_Y+6, POP_X+6, "(0) Continue");
cprint(POP_Y+3+v->printmode, POP_X+5, ">");
wait_keyup();
while (!sflag) {
switch(get_key()) {
case 2:
/* Separate Addresses */
v->printmode=PRINTMODE_ADDRESSES;
v->eadr = 0;
sflag++;
break;
case 3:
/* BadRAM Patterns */
v->printmode=PRINTMODE_PATTERNS;
sflag++;
prt++;
break;
case 4:
/* Error Counts Only */
v->printmode=PRINTMODE_NONE;
sflag++;
break;
case 11:
case 57:
/* 0/CR - Continue */
sflag++;
break;
}
}
popclear();
break;
case 7:
/* 6 - ECC Polling Mode */
popclear();
cprint(POP_Y+1, POP_X+2, "ECC Polling Mode:");
cprint(POP_Y+3, POP_X+6, "(1) Recommended");
cprint(POP_Y+4, POP_X+6, "(2) On");
cprint(POP_Y+5, POP_X+6, "(3) Off");
cprint(POP_Y+6, POP_X+6, "(0) Continue");
wait_keyup();
while(!sflag) {
switch(get_key()) {
case 2:
set_ecc_polling(-1);
sflag++;
break;
case 3:
set_ecc_polling(1);
sflag++;
break;
case 4:
set_ecc_polling(0);
sflag++;
break;
case 11:
case 57:
/* 0/CR - Continue */
sflag++;
break;
}
}
popclear();
break;
case 8:
wait_keyup();
restart();
break;
case 9:
reprint_screen = 1;
flag++;
break;
case 10:
get_menu();
break;
case 11:
case 57:
case 28:
/* 0/CR/SP - Continue */
flag++;
break;
}
}
popdown();
if (prt) {
printpatn();
}
if (reprint_screen){
tty_print_screen();
}
}
void get_config()
{
int flag = 0, sflag = 0, i, prt = 0;
int reprint_screen = 0;
ulong page;
popup();
wait_keyup();
while(!flag) {
cprint(POP_Y+1, POP_X+2, "Settings:");
cprint(POP_Y+3, POP_X+6, "(1) Test Selection");
cprint(POP_Y+4, POP_X+6, "(2) Address Range");
cprint(POP_Y+5, POP_X+6, "(3) Memory Sizing");
cprint(POP_Y+6, POP_X+6, "(4) Error Report Mode");
cprint(POP_Y+7, POP_X+6, "(5) Show DMI Memory Info");
cprint(POP_Y+8, POP_X+6, "(6) ECC Mode");
cprint(POP_Y+9, POP_X+6, "(7) Restart");
cprint(POP_Y+10, POP_X+6, "(8) Refresh Screen");
//cprint(POP_Y+11, POP_X+6, "(9) Display SPD Data");
cprint(POP_Y+11, POP_X+6, "(9) Display Consecutive");
cprint(POP_Y+12, POP_X+6, " Failing Address Data");
cprint(POP_Y+13, POP_X+6, "(0) Continue");
/* Wait for key release */
/* Fooey! This nuts'es up the serial input. */
sflag = 0;
switch(get_key()) {
case 2:
/* 1 - Test Selection */
popclear();
cprint(POP_Y+1, POP_X+2, "Test Selection:");
cprint(POP_Y+3, POP_X+6, "(1) Default Tests");
cprint(POP_Y+4, POP_X+6, "(2) Skip Current Test");
cprint(POP_Y+5, POP_X+6, "(3) Select Test");
cprint(POP_Y+6, POP_X+6, "(4) Select Bit Fade Test");
//cprint(POP_Y+7, POP_X+6, "(5) Select Uncached Test");
cprint(POP_Y+8, POP_X+6, "(0) Continue");
if (v->testsel < 0) {
cprint(POP_Y+3, POP_X+5, ">");
} else {
cprint(POP_Y+5, POP_X+5, ">");
}
wait_keyup();
while (!sflag) {
switch(get_key()) {
case 2:
/* Default */
if (v->testsel >= 9) {
bail++;
}
v->testsel = -1;
find_ticks_for_pass();
sflag++;
cprint(LINE_INFO, COL_TST, "Std");
break;
case 3:
/* Skip test */
bail++;
sflag++;
break;
case 4:
/* Select test */
popclear();
cprint(POP_Y+1, POP_X+3,
"Test Selection:");
cprint(POP_Y+4, POP_X+5,
"Test Number [0-9]: ");
i = getval(POP_Y+4, POP_X+24, 0);
if (i <= 9) {
if (i != v->testsel) {
v->pass = -1;
v->test = -1;
}
v->testsel = i;
}
find_ticks_for_pass();
sflag++;
bail++;
cprint(LINE_INFO, COL_TST, "#");
dprint(LINE_INFO, COL_TST+1, i, 2, 1);
break;
case 5:
if (v->testsel != 9) {
v->pass = -1;
v->test = -1;
}
v->testsel = 9;
find_ticks_for_pass();
sflag++;
bail++;
cprint(LINE_INFO, COL_TST, "#");
dprint(LINE_INFO, COL_TST+1, 9, 3, 1);
break;
/*
case 6:
if (v->testsel != 10) {
v->pass = -1;
v->test = -1;
}
v->testsel = 9+1;
find_ticks_for_pass();
sflag++;
bail++;
cprint(LINE_INFO, COL_TST, "#");
dprint(LINE_INFO, COL_TST+1, 10, 3, 1);
break;
*/
case 11:
case 57:
sflag++;
break;
}
}
popclear();
break;
case 3:
/* 2 - Address Range */
popclear();
cprint(POP_Y+1, POP_X+2, "Test Address Range:");
cprint(POP_Y+3, POP_X+6, "(1) Set Lower Limit");
cprint(POP_Y+4, POP_X+6, "(2) Set Upper Limit");
cprint(POP_Y+5, POP_X+6, "(3) Test All Memory");
cprint(POP_Y+6, POP_X+6, "(0) Continue");
wait_keyup();
while (!sflag) {
switch(get_key()) {
case 2:
/* Lower Limit */
popclear();
cprint(POP_Y+2, POP_X+4,
"Lower Limit: ");
cprint(POP_Y+4, POP_X+4,
"Current: ");
aprint(POP_Y+4, POP_X+13, v->plim_lower);
cprint(POP_Y+6, POP_X+4,
"New: ");
page = getval(POP_Y+6, POP_X+9, 12);
if (page + 1 <= v->plim_upper) {
v->plim_lower = page;
v->test--;
bail++;
}
adj_mem();
find_ticks_for_pass();
sflag++;
break;
case 3:
/* Upper Limit */
popclear();
cprint(POP_Y+2, POP_X+4,
"Upper Limit: ");
cprint(POP_Y+4, POP_X+4,
"Current: ");
aprint(POP_Y+4, POP_X+13, v->plim_upper);
cprint(POP_Y+6, POP_X+4,
"New: ");
page = getval(POP_Y+6, POP_X+9, 12);
if (page - 1 >= v->plim_lower) {
v->plim_upper = page;
v->test--;
bail++;
}
adj_mem();
find_ticks_for_pass();
sflag++;
break;
case 4:
/* All of memory */
v->plim_lower = 0;
v->plim_upper = v->pmap[v->msegs - 1].end;
v->test--;
bail++;
adj_mem();
find_ticks_for_pass();
sflag++;
break;
case 11:
case 57:
/* 0/CR - Continue */
sflag++;
break;
}
}
popclear();
break;
case 4:
/* 3 - Memory Sizing */
popclear();
cprint(POP_Y+1, POP_X+2, "Memory Sizing:");
cprint(POP_Y+3, POP_X+6, "(1) BIOS - Std");
cprint(POP_Y+4, POP_X+6, "(2) Probe");
cprint(POP_Y+5, POP_X+6, "(0) Continue");
if(!e820_nr){
if (memsz_mode == SZ_MODE_BIOS) {
cprint(POP_Y+3, POP_X+5, ">");
} else {
cprint(POP_Y+4, POP_X+5, ">");
}
}
wait_keyup();
while (!sflag) {
switch(get_key()) {
case 2:
memsz_mode = SZ_MODE_BIOS;
wait_keyup();
restart();
break;
case 3:
memsz_mode = SZ_MODE_PROBE;
wait_keyup();
restart();
break;
case 11:
case 57:
/* 0/CR - Continue */
sflag++;
break;
}
}
popclear();
break;
case 5:
/* 4 - Show error Mode */
popclear();
cprint(POP_Y+1, POP_X+2, "Printing Mode:");
cprint(POP_Y+3, POP_X+6, "(1) Error Summary");
cprint(POP_Y+4, POP_X+6, "(2) Individual Errors");
cprint(POP_Y+5, POP_X+6, "(3) BadRAM Patterns");
cprint(POP_Y+6, POP_X+6, "(4) Error Counts Only");
cprint(POP_Y+7, POP_X+6, "(5) DMI Device Name");
cprint(POP_Y+8, POP_X+6, "(6) Beep on Error");
cprint(POP_Y+10, POP_X+6, "(0) Cancel");
cprint(POP_Y+3+v->printmode, POP_X+5, ">");
if (beepmode) { cprint(POP_Y+8, POP_X+5, ">"); }
wait_keyup();
while (!sflag) {
switch(get_key()) {
case 2:
/* Error Summary */
v->printmode=PRINTMODE_SUMMARY;
v->erri.eadr = 0;
v->erri.hdr_flag = 0;
sflag++;
break;
case 3:
/* Separate Addresses */
v->printmode=PRINTMODE_ADDRESSES;
v->erri.eadr = 0;
v->erri.hdr_flag = 0;
v->msg_line = LINE_SCROLL-1;
sflag++;
break;
case 4:
/* BadRAM Patterns */
v->printmode=PRINTMODE_PATTERNS;
v->erri.hdr_flag = 0;
sflag++;
prt++;
break;
case 5:
/* Error Counts Only */
v->printmode=PRINTMODE_NONE;
v->erri.hdr_flag = 0;
sflag++;
break;
case 6:
/* Error Counts Only */
v->printmode=PRINTMODE_DMI;
v->erri.hdr_flag = 0;
sflag++;
break;
case 7:
/* Set Beep On Error mode */
beepmode = !beepmode;
sflag++;
break;
case 11:
case 57:
/* 0/CR - Continue */
sflag++;
break;
}
}
popclear();
break;
case 6:
/* Display DMI Memory Info */
pop2up();
print_dmi_info();
pop2down();
break;
case 7:
/* 6 - ECC Polling Mode */
popclear();
cprint(POP_Y+1, POP_X+2, "ECC Polling Mode:");
cprint(POP_Y+3, POP_X+6, "(1) Recommended");
cprint(POP_Y+4, POP_X+6, "(2) On");
cprint(POP_Y+5, POP_X+6, "(3) Off");
cprint(POP_Y+6, POP_X+6, "(0) Continue");
wait_keyup();
while(!sflag) {
switch(get_key()) {
case 2:
set_ecc_polling(-1);
sflag++;
break;
case 3:
set_ecc_polling(1);
sflag++;
break;
case 4:
set_ecc_polling(0);
sflag++;
break;
case 11:
case 57:
/* 0/CR - Continue */
sflag++;
break;
}
}
popclear();
break;
case 8:
wait_keyup();
restart();
break;
case 9:
reprint_screen = 1;
flag++;
break;
case 10:
//XXX was spddata
//popdown();
//show_spd();
//popup();
//sflag++;
//XXX was spddata ^
//Display Failing Address Data
popclear();
wait_keyup();
int err_idx = 0;
cprint(POP_Y+1, POP_X+2, "Consecutive Failing Addresses:");
cprint(POP_Y+3, POP_X+14, " of ");
dprint(POP_Y+3, POP_X+19, v->err_range.size,4,0);
cprint(POP_Y+5, POP_X+6, "Errors in range: ");
cprint(POP_Y+6, POP_X+6, "Range Stride: ");
cprint(POP_Y+7, POP_X+6, "High Address: 0x");
cprint(POP_Y+8, POP_X+6, "Low Address: 0x");
cprint(POP_Y+9, POP_X+6, "Histogram of faulty bits: <-bit 31, bit 0 ->");
cprint(POP_Y+12, POP_X+6, "Hit 1 to Continue, 0 to quit"); //option 1
//cprint(POP_Y+12, POP_X+6, "Hit a key to Continue"); //option 2
i = 1;
int j = 0;
int mag;
ulong h;
//loop through all records
while ((i==1) && (err_idx<v->err_range.size)){
dprint(POP_Y+3, POP_X+6, err_idx+1,8,0);//number
hprint(POP_Y+5, POP_X+22, v->err_range.ranges[err_idx].count_per_range);//err count per range
hprint(POP_Y+6, POP_X+22, v->err_range.ranges[err_idx].range_stride);//stride per range
hprint(POP_Y+7, POP_X+22, v->err_range.ranges[err_idx].high_addr);//high addr
hprint(POP_Y+8, POP_X+22, v->err_range.ranges[err_idx].low_addr);//low addr
//print histogram
for (j=0;j<32;j++){
mag = 0;
h = v->err_range.ranges[err_idx].hist[j];
while (h>0){
mag++;
h = h>>1;
}
dprint(POP_Y+10, POP_X+6+(j*5), mag,4,0);
}
i = getval(POP_Y+12, POP_X+34, 0); //option 1
//wait_keyup(); //option 2
err_idx++;
}
//popup();
popclear();
sflag++;
break;
case 11:
case 57:
case 28:
/* 0/CR/SP - Continue */
flag++;
break;
}
}
popdown();
if (prt) {
printpatn();
}
if (reprint_screen){
tty_print_screen();
}
}
static int newmt(void)
{
int i = 0, j = 0;
unsigned long chunks;
unsigned long lo, hi;
#if NMOD_FRAMEBUFFER > 0
video_cls();
#endif
if(setjmp(jmpb_mt)&&(returncode==2)){
ioctl (STDIN, TCSETAF, &sav);
firsttime = 0;
v->test = 0;
v->pass = 0;
v->msg_line = 0;
v->ecount = 0;
v->ecc_ecount = 0;
autotest=0;
firsttime=0;
/* Clear the screen */
#if NMOD_FRAMEBUFFER > 0
video_cls();
#endif
return 0;
}
ioctl (STDIN, CBREAK, &sav);
while(1)
{
window=0;
/* If first time, initialize test */
windows[0].start =LOW_TEST_ADR>>12;
windows[0].end= HIGH_TEST_ADR>>12;
if(!firsttime){init();firsttime++;}
bail = 0;
/* Find the memory areas I am going to test */
compute_segments(window);
if (segs == 0) {
goto skip_window;
}
/* Now map in the window... */
if (map_page(v->map[0].pbase_addr) < 0) {
goto skip_window;
}
/* Update display of memory segments being tested */
lo = page_of(v->map[0].start);
hi = page_of(v->map[segs -1].end);
aprint(LINE_RANGE, COL_MID+9, lo-0x80000);
cprint(LINE_RANGE, COL_MID+14, " - ");
aprint(LINE_RANGE, COL_MID+17, hi-0x80000);
aprint(LINE_RANGE, COL_MID+23, v->selected_pages);
cprint(LINE_RANGE, COL_MID+28,
((ulong)&_start == LOW_TEST_ADR)?" ":" Relocated");
/* Now setup the test parameters based on the current test number */
/* Figure out the next test to run */
if (v->testsel >= 0) {
v->test = v->testsel;
}
dprint(LINE_TST, COL_MID+6, v->test, 2, 1);
cprint(LINE_TST, COL_MID+9, tseq[v->test].msg);
set_cache(tseq[v->test].cache);
/* Compute the number of SPINSZ memory segments */
chunks = 0;
for(i = 0; i < segs; i++) {
unsigned long len;
len = v->map[i].end - v->map[i].start;
chunks += (len + SPINSZ -1)/SPINSZ;
}
test_ticks = find_ticks_for_test(chunks, v->test);
nticks = 0;
v->tptr = 0;
cprint(1, COL_MID+8, " ");
switch(tseq[v->test].pat) {
/* Now do the testing according to the selected pattern */
case 0: /* Moving inversions, all ones and zeros */
p1 = 0;
p2 = ~p1;
movinv1(tseq[v->test].iter,p1,p2);
BAILOUT;
/* Switch patterns */
p2 = p1;
p1 = ~p2;
movinv1(tseq[v->test].iter,p1,p2);
BAILOUT;
break;
case 1: /* Moving inversions, 8 bit wide walking ones and zeros. */
p0 = 0x80;
for (i=0; i<8; i++, p0=p0>>1) {
p1 = p0 | (p0<<8) | (p0<<16) | (p0<<24);
p2 = ~p1;
movinv1(tseq[v->test].iter,p1,p2);
BAILOUT;
/* Switch patterns */
p2 = p1;
p1 = ~p2;
movinv1(tseq[v->test].iter,p1,p2);
BAILOUT
}
break;
case 2: /* Moving inversions, 32 bit shifting pattern, very long */
{
u_int32_t pa = 0;
for (i=0, pa=1; pa; pa=pa<<1, i++) {
movinv32(tseq[v->test].iter,pa, 1, 0x80000000, 0, i);
BAILOUT
movinv32(tseq[v->test].iter,~pa, 0xfffffffe,
0x7fffffff, 1, i);
BAILOUT
}
}
break;
case 3: /* Modulo X check, all ones and zeros */
p1=0;
for (i=0; i<MOD_SZ; i++) {
p2 = ~p1;
modtst(i, tseq[v->test].iter, p1, p2);
BAILOUT
/* Switch patterns */
p2 = p1;
p1 = ~p2;
modtst(i, tseq[v->test].iter, p1,p2);
BAILOUT
}
break;
case 4: /* Modulo X check, 8 bit pattern */
p0 = 0x80;
for (j=0; j<8; j++, p0=p0>>1) {
p1 = p0 | (p0<<8) | (p0<<16) | (p0<<24);
for (i=0; i<MOD_SZ; i++) {
p2 = ~p1;
modtst(i, tseq[v->test].iter, p1, p2);
BAILOUT
/* Switch patterns */
p2 = p1;
p1 = ~p2;
modtst(i, tseq[v->test].iter, p1, p2);
BAILOUT
}
}
break;
case 5: /* Address test, walking ones */
addr_tst1();
BAILOUT;
break;
case 6: /* Address test, own address */
addr_tst2();
BAILOUT;
break;
case 7: /* Block move test */
block_move(tseq[v->test].iter);
BAILOUT;
break;
case 8: /* Bit fade test */
if (window == 0 ) {
bit_fade();
}
BAILOUT;
break;
case 9: /* Random Data Sequence */
for (i=0; i < tseq[v->test].iter; i++) {
movinvr();
BAILOUT;
}
break;
case 10: /* Random Data */
for (i=0; i < tseq[v->test].iter; i++) {
p1 = rand();
p2 = ~p1;
movinv1(2,p1,p2);
BAILOUT;
}
break;
}
skip_window:
if (bail) {
goto bail_test;
}
/* Rever to the default mapping and enable the cache */
paging_off();
set_cache(1);
window++;
if (window >= sizeof(windows)/sizeof(windows[0])) {
window = 0;
}
/* We finished the test so clear the pattern */
cprint(LINE_PAT, COL_PAT, " ");
skip_test:
v->test++;
bail_test:
paging_off();
set_cache(1);
check_input();
window = 0;
cprint(LINE_PAT, COL_PAT-3, " ");
/* If this was the last test then we finished a pass */
if (v->test >= DEFTESTS || v->testsel >= 0) {
v->pass++;
dprint(LINE_INFO, COL_PASS, v->pass, 5, 0);
v->test = 0;
v->total_ticks = 0;
v->pptr = 0;
cprint(0, COL_MID+8,
" ");
}
}
return 0;
}
void get_config()
{
int flag = 0, sflag = 0, i, j, k, n, m, prt = 0;
int reprint_screen = 0;
char cp[64];
ulong page;
popup();
wait_keyup();
while(!flag) {
cprint(POP_Y+1, POP_X+2, "Settings:");
cprint(POP_Y+3, POP_X+4, "(1) Select wat MEMEZ to test");
cprint(POP_Y+4, POP_X+4, "(2) Address Range");
cprint(POP_Y+5, POP_X+4, "(3) O NOES ERRORZ Mode");
cprint(POP_Y+6, POP_X+4, "(4) Select with COREZ 2 test");
cprint(POP_Y+7, POP_X+4, "(5) Refresh Screen");
cprint(POP_Y+8, POP_X+4, "(6) DISPLYUZ DMI DATUZ");
cprint(POP_Y+9, POP_X+4, "(7) such RAM much SPD");
cprint(POP_Y+11, POP_X+4, "(0) Continue rowHAMMER TIME");
/* Wait for key release */
/* Fooey! This nuts'es up the serial input. */
sflag = 0;
switch(get_key()) {
case 2:
/* 1 - Test Selection */
popclear();
cprint(POP_Y+1, POP_X+2, "Test Selection:");
cprint(POP_Y+3, POP_X+6, "(1) Default Tests");
cprint(POP_Y+4, POP_X+6, "(2) Skip Current Test");
cprint(POP_Y+5, POP_X+6, "(3) Select Test");
cprint(POP_Y+6, POP_X+6, "(4) Enter Test List");
cprint(POP_Y+7, POP_X+6, "(0) Cancel");
if (v->testsel < 0) {
cprint(POP_Y+3, POP_X+5, ">");
} else {
cprint(POP_Y+5, POP_X+5, ">");
}
wait_keyup();
while (!sflag) {
switch(get_key()) {
case 2:
/* Default - All tests */
i = 0;
while (tseq[i].cpu_sel) {
tseq[i].sel = 1;
i++;
}
find_ticks_for_pass();
sflag++;
break;
case 3:
/* Skip test */
bail++;
sflag++;
break;
case 4:
/* Select test */
popclear();
cprint(POP_Y+1, POP_X+3,
"Test Selection:");
cprint(POP_Y+4, POP_X+5,
"Test Number [1-11]: ");
n = getval(POP_Y+4, POP_X+24, 0) - 1;
if (n <= 11)
{
/* Deselect all tests */
i = 0;
while (tseq[i].cpu_sel) {
tseq[i].sel = 0;
i++;
}
/* Now set the selection */
tseq[n].sel = 1;
v->pass = -1;
test = n;
find_ticks_for_pass();
sflag++;
bail++;
}
break;
case 5:
/* Enter a test list */
popclear();
cprint(POP_Y+1, POP_X+3,
"Enter a comma separated list");
cprint(POP_Y+2, POP_X+3,
"of tests to execute:");
cprint(POP_Y+5, POP_X+5, "List: ");
/* Deselect all tests */
k = 0;
while (tseq[k].cpu_sel) {
tseq[k].sel = 0;
k++;
}
/* Get the list */
for (i=0; i<64; i++) cp[i] = 0;
get_list(POP_Y+5, POP_X+10, 64, cp);
/* Now enable all of the tests in the
* list */
i = j = m = 0;
while (1) {
if (isdigit(cp[i])) {
n = cp[i]-'0';
j = j*10 + n;
i++;
if (cp[i] == ',' || cp[i] == 0){
if (j < k) {
tseq[j].sel = 1;
m++;
}
if (cp[i] == 0) break;
j = 0;
i++;
}
}
}
/* If we didn't select at least one
* test turn them all back on */
if (m == 0) {
k = 0;
while (tseq[k].cpu_sel) {
tseq[k].sel = 1;
k++;
}
}
v->pass = -1;
test = n;
find_ticks_for_pass();
sflag++;
bail++;
break;
case 11:
case 57:
sflag++;
break;
}
}
popclear();
break;
case 3:
/* 2 - Address Range */
popclear();
cprint(POP_Y+1, POP_X+2, "rowHAMMER TIME Address Range:");
cprint(POP_Y+3, POP_X+6, "(1) Set Lower Limit");
cprint(POP_Y+4, POP_X+6, "(2) Set Upper Limit");
cprint(POP_Y+5, POP_X+6, "(3) Test All Memory");
cprint(POP_Y+6, POP_X+6, "(0) Cancel");
wait_keyup();
while (!sflag) {
switch(get_key()) {
case 2:
/* Lower Limit */
popclear();
cprint(POP_Y+2, POP_X+4,
"Lower Limit: ");
cprint(POP_Y+4, POP_X+4,
"Current: ");
aprint(POP_Y+4, POP_X+13, v->plim_lower);
cprint(POP_Y+6, POP_X+4,
"New: ");
page = getval(POP_Y+6, POP_X+9, 12);
if (page + 1 <= v->plim_upper) {
v->plim_lower = page;
test--;
bail++;
}
adj_mem();
find_chunks();
find_ticks_for_pass();
sflag++;
break;
case 3:
/* Upper Limit */
popclear();
cprint(POP_Y+2, POP_X+4,
"Upper Limit: ");
cprint(POP_Y+4, POP_X+4,
"Current: ");
aprint(POP_Y+4, POP_X+13, v->plim_upper);
cprint(POP_Y+6, POP_X+4,
"New: ");
page = getval(POP_Y+6, POP_X+9, 12);
if (page - 1 >= v->plim_lower) {
v->plim_upper = page;
bail++;
test--;
}
adj_mem();
find_chunks();
find_ticks_for_pass();
sflag++;
break;
case 4:
/* All of memory */
v->plim_lower = 0;
v->plim_upper =
v->pmap[v->msegs - 1].end;
test--;
bail++;
adj_mem();
find_chunks();
find_ticks_for_pass();
sflag++;
break;
case 11:
case 57:
/* 0/CR - Continue */
sflag++;
break;
}
}
popclear();
break;
case 4:
/* Error Mode */
popclear();
cprint(POP_Y+1, POP_X+2, "Printing Mode:");
cprint(POP_Y+3, POP_X+6, "(1) O NOES ALL ERRORZ");
cprint(POP_Y+4, POP_X+6, "(2) O NOES ONE ERRORZ");
cprint(POP_Y+5, POP_X+6, "(3) BadRAM Patterns. BADRAM");
cprint(POP_Y+6, POP_X+6, "(4) O NOES HOW MANYZ ERRORZ");
cprint(POP_Y+7, POP_X+6, "(5) BEEP BEEP BEEP ERRORZ");
cprint(POP_Y+8, POP_X+6, "(0) GTFO");
cprint(POP_Y+3+v->printmode, POP_X+5, ">");
if (beepmode) { cprint(POP_Y+7, POP_X+5, ">"); }
wait_keyup();
while (!sflag) {
switch(get_key()) {
case 2:
/* Error Summary */
v->printmode=PRINTMODE_SUMMARY;
v->erri.eadr = 0;
v->erri.hdr_flag = 0;
sflag++;
break;
case 3:
/* Separate Addresses */
v->printmode=PRINTMODE_ADDRESSES;
v->erri.eadr = 0;
v->erri.hdr_flag = 0;
v->msg_line = LINE_SCROLL-1;
sflag++;
break;
case 4:
/* BadRAM Patterns */
v->printmode=PRINTMODE_PATTERNS;
v->erri.hdr_flag = 0;
sflag++;
prt++;
break;
case 5:
/* Error Counts Only */
v->printmode=PRINTMODE_NONE;
v->erri.hdr_flag = 0;
sflag++;
break;
case 6:
/* Set Beep On Error mode */
beepmode = !beepmode;
sflag++;
break;
case 11:
case 57:
/* 0/CR - Continue */
sflag++;
break;
}
}
popclear();
break;
case 5:
/* CPU Mode */
reprint_screen = 1;
popclear();
cprint(POP_Y+1, POP_X+2, "BRAINE Selection Mode:");
cprint(POP_Y+3, POP_X+6, "(1) Parallel (All)");
cprint(POP_Y+4, POP_X+6, "(2) Round Robin Hood (RRbH)");
cprint(POP_Y+5, POP_X+6, "(3) Sequential (Seq)");
cprint(POP_Y+6, POP_X+6, "(0) NOPE BYE");
cprint(POP_Y+2+cpu_mode, POP_X+5, ">");
wait_keyup();
while(!sflag) {
switch(get_key()) {
case 2:
if (cpu_mode != CPM_ALL) bail++;
cpu_mode = CPM_ALL;
sflag++;
popdown();
cprint(9,34,"All");
popup();
break;
case 3:
if (cpu_mode != CPM_RROBIN) bail++;
cpu_mode = CPM_RROBIN;
sflag++;
popdown();
cprint(9,34,"RRb");
popup();
break;
case 4:
if (cpu_mode != CPM_SEQ) bail++;
cpu_mode = CPM_SEQ;
sflag++;
popdown();
cprint(9,34,"Seq");
popup();
break;
case 11:
case 57:
/* 0/CR - Continue */
sflag++;
break;
}
}
popclear();
break;
case 6:
reprint_screen = 1;
flag++;
break;
case 7:
/* Display DMI Memory Info */
pop2up();
print_dmi_info();
pop2down();
break;
case 8:
/* Display SPD Data */
popdown();
show_spd();
popup();
sflag++;
break;
case 11:
case 57:
case 28:
/* 0/CR/SP - Continue */
flag++;
break;
}
}
popdown();
if (prt) {
printpatn();
}
if (reprint_screen){
tty_print_screen();
}
}
void mainloop
// ====================================================================
//
// purpos : 2-dimensional diffusion equation solved by FDM
//
// date : 2012-5-10
// programmer : Michel Müller
// place : Tokyo Institute of Technology
//
(
FLOAT *f, /* dependent variable */
FLOAT *fn, /* updated dependent variable */
FLOAT kappa, /* diffusion coefficient */
FLOAT *time, /* time */
FLOAT dt, /* time step interval */
FLOAT dx, /* grid spacing in the x-direction */
FLOAT dy, /* grid spacing in the y-direction */
FLOAT dz /* grid spacing in the z-direction */
)
// --------------------------------------------------------------------
{
int icnt = 1;
double start_time, elapsed_time;
double start_time_total, start_computation_time, elapsed_time_total, elapsed_computation_time;
clock_t ctime_start_computation_time, ctime_start_total_time;
double ctime_elapsed_computation_time, ctime_elapsed_total_time;
long long int numOfStencilsComputed = 0;
long long int idealCacheModelBytesTransferred = 0;
long long int noCacheModelBytesTransferred = 0;
start_time = omp_get_wtime();
ctime_start_total_time = clock() / CLOCKS_PER_SEC;
printf("Starting Reference C Version of 3D Diffusion\n");
printf("kappa: %e, dt: %e, dx: %e\n", kappa, dt, dx);
#pragma omp parallel
#pragma omp master
{
printf("num threads: %d\n", omp_get_num_threads( ));
}
#pragma acc data copy(f[0:XYZ_SIZE]), create(fn[0:XYZ_SIZE])
{
#pragma omp master
{
start_computation_time = omp_get_wtime();
ctime_start_computation_time = clock() / CLOCKS_PER_SEC;
}
do { if(icnt % 100 == 0) fprintf(stderr,"time after iteration %4d:%7.5f\n",icnt+1,*time + dt);
diffusion3d(f,fn,kappa,dt,dx,dy,dz);
numOfStencilsComputed += DIM_X_INNER * DIM_Y_INNER * DIM_Z_INNER;
idealCacheModelBytesTransferred += DIM_X_INNER * DIM_Y_INNER * DIM_Z_INNER * FLOAT_BYTE_LENGTH * 2;
noCacheModelBytesTransferred += DIM_X_INNER * DIM_Y_INNER * DIM_Z_INNER * FLOAT_BYTE_LENGTH * 8;
swap(&f,&fn);
*time = *time + dt;
} while(icnt++ < 90000 && *time + 0.5*dt < 0.1);
#pragma acc wait
#pragma omp master
{
elapsed_computation_time = omp_get_wtime() - start_computation_time;
ctime_elapsed_computation_time = (clock() - ctime_start_computation_time) / (double) CLOCKS_PER_SEC;
}
}
elapsed_time_total = omp_get_wtime() - start_time;
ctime_elapsed_total_time = (clock() - ctime_start_total_time) / (double) CLOCKS_PER_SEC;
double elapsed_computation_time_combined = elapsed_computation_time;
if (elapsed_computation_time_combined <= 0.0) {
elapsed_computation_time_combined = ctime_elapsed_computation_time;
}
aprint("Calculated Time= %9.3e [sec]\n",*time);
aprint("Elapsed Total Time (OMP timer)= %9.3e [sec]\n",elapsed_time_total);
aprint("Elapsed Total Time (CTime)= %9.3e [sec]\n",ctime_elapsed_total_time);
aprint("Elapsed Computation Time (OMP timer)= %9.3e [sec]\n",elapsed_computation_time);
aprint("Elapsed Computation Time (CTime)= %9.3e [sec]\n",ctime_elapsed_computation_time);
aprint("Performance= %7.2f [million stencils/sec]\n",((double)numOfStencilsComputed)/elapsed_computation_time_combined*1.0e-06);
aprint("Bandwidth Ideal Cache Model= %7.2f [GB/s]\n",((double)idealCacheModelBytesTransferred)/elapsed_computation_time_combined*1.0e-09);
aprint("Bandwidth No Cache Model= %7.2f [GB/s]\n",((double)noCacheModelBytesTransferred)/elapsed_computation_time_combined*1.0e-09);
}
