1d3ae85c4SBarry Smith 2d3ae85c4SBarry Smith # include <stdio.h> 3d3ae85c4SBarry Smith # include <math.h> 4d3ae85c4SBarry Smith # include <limits.h> 5d3ae85c4SBarry Smith # include <float.h> 6d3ae85c4SBarry Smith 7d3ae85c4SBarry Smith /* 8d3ae85c4SBarry Smith * Program: Stream 9d3ae85c4SBarry Smith * Programmer: Joe R. Zagar 10d3ae85c4SBarry Smith * Revision: 4.0-BETA, October 24, 1995 11d3ae85c4SBarry Smith * Original code developed by John D. McCalpin 12d3ae85c4SBarry Smith * 13d3ae85c4SBarry Smith * This program measures memory transfer rates in MB/s for simple 14d3ae85c4SBarry Smith * computational kernels coded in C. These numbers reveal the quality 15d3ae85c4SBarry Smith * of code generation for simple uncacheable kernels as well as showing 16d3ae85c4SBarry Smith * the cost of floating-point operations relative to memory accesses. 17d3ae85c4SBarry Smith * 18d3ae85c4SBarry Smith * INSTRUCTIONS: 19d3ae85c4SBarry Smith * 20d3ae85c4SBarry Smith * 1) Stream requires a good bit of memory to run. Adjust the 21d3ae85c4SBarry Smith * value of 'N' (below) to give a 'timing calibration' of 22d3ae85c4SBarry Smith * at least 20 clock-ticks. This will provide rate estimates 23d3ae85c4SBarry Smith * that should be good to about 5% precision. 24d3ae85c4SBarry Smith */ 25d3ae85c4SBarry Smith 26d3ae85c4SBarry Smith # define N 2000000 27d3ae85c4SBarry Smith # define NTIMES 50 28d3ae85c4SBarry Smith # define OFFSET 0 29d3ae85c4SBarry Smith 30d3ae85c4SBarry Smith /* 31d3ae85c4SBarry Smith * 3) Compile the code with full optimization. Many compilers 32d3ae85c4SBarry Smith * generate unreasonably bad code before the optimizer tightens 33d3ae85c4SBarry Smith * things up. If the results are unreasonably good, on the 34d3ae85c4SBarry Smith * other hand, the optimizer might be too smart for me! 35d3ae85c4SBarry Smith * 36d3ae85c4SBarry Smith * Try compiling with: 37d3ae85c4SBarry Smith * cc -O stream_d.c second.c -o stream_d -lm 38d3ae85c4SBarry Smith * 39d3ae85c4SBarry Smith * This is known to work on Cray, SGI, IBM, and Sun machines. 40d3ae85c4SBarry Smith * 41d3ae85c4SBarry Smith * 42d3ae85c4SBarry Smith * 4) Mail the results to mccalpin@cs.virginia.edu 43d3ae85c4SBarry Smith * Be sure to include: 44d3ae85c4SBarry Smith * a) computer hardware model number and software revision 45d3ae85c4SBarry Smith * b) the compiler flags 46d3ae85c4SBarry Smith * c) all of the output from the test case. 47d3ae85c4SBarry Smith * Thanks! 48d3ae85c4SBarry Smith * 49d3ae85c4SBarry Smith */ 50d3ae85c4SBarry Smith 51d3ae85c4SBarry Smith # define HLINE "-------------------------------------------------------------\n" 52d3ae85c4SBarry Smith 53d3ae85c4SBarry Smith # ifndef MIN 54d3ae85c4SBarry Smith # define MIN(x,y) ((x)<(y) ? (x) : (y)) 55d3ae85c4SBarry Smith # endif 56d3ae85c4SBarry Smith # ifndef MAX 57d3ae85c4SBarry Smith # define MAX(x,y) ((x)>(y) ? (x) : (y)) 58d3ae85c4SBarry Smith # endif 59d3ae85c4SBarry Smith 60d3ae85c4SBarry Smith static double a[N+OFFSET], 61d3ae85c4SBarry Smith b[N+OFFSET], 62d3ae85c4SBarry Smith c[N+OFFSET]; 63d3ae85c4SBarry Smith /*double *a,*b,*c;*/ 64d3ae85c4SBarry Smith 65d3ae85c4SBarry Smith static double mintime[4] = {FLT_MAX,FLT_MAX,FLT_MAX,FLT_MAX}; 66d3ae85c4SBarry Smith 67d3ae85c4SBarry Smith static const char *label[4] = {"Copy: ", "Scale: ", "Add: ", "Triad: "}; 68d3ae85c4SBarry Smith 69d3ae85c4SBarry Smith static double bytes[4] = { 70d3ae85c4SBarry Smith 2 * sizeof(double) * N, 71d3ae85c4SBarry Smith 2 * sizeof(double) * N, 72d3ae85c4SBarry Smith 3 * sizeof(double) * N, 73d3ae85c4SBarry Smith 3 * sizeof(double) * N 74d3ae85c4SBarry Smith }; 75d3ae85c4SBarry Smith 76e109280bSBarry Smith #include <mpi.h> 77d3ae85c4SBarry Smith 78d3ae85c4SBarry Smith int main(int argc,char **args) 79d3ae85c4SBarry Smith { 80d1d3a73cSBarry Smith int quantum, checktick(void); 81d3ae85c4SBarry Smith register int j, k; 82d3ae85c4SBarry Smith double scalar, t, times[4][NTIMES],irate[4],rate[4]; 83d3ae85c4SBarry Smith int rank,size,resultlen; 84d3ae85c4SBarry Smith char hostname[MPI_MAX_PROCESSOR_NAME]; 851df1832dSBarry Smith MPI_Status status; 86*b7250d5dSSatish Balay int ierr=0; 87d3ae85c4SBarry Smith 88d3ae85c4SBarry Smith MPI_Init(&argc,&args); 89d3ae85c4SBarry Smith MPI_Comm_rank(MPI_COMM_WORLD,&rank); 90d3ae85c4SBarry Smith MPI_Comm_size(MPI_COMM_WORLD,&size); 91436f0324SBarry Smith if (!rank) printf("Number of MPI processes %d ",size); 92d3ae85c4SBarry Smith 936b58a888SBarry Smith for (j=0; j<MPI_MAX_PROCESSOR_NAME; j++) { 946b58a888SBarry Smith hostname[j] = 0; 956b58a888SBarry Smith } 96d3ae85c4SBarry Smith MPI_Get_processor_name(hostname,&resultlen); 971df1832dSBarry Smith if (!rank) { 98436f0324SBarry Smith printf("Processor names %s ",hostname); 991df1832dSBarry Smith for (j=1; j<size; j++) { 1001df1832dSBarry Smith MPI_Recv(hostname,MPI_MAX_PROCESSOR_NAME,MPI_CHAR,j,0,MPI_COMM_WORLD,&status); 101436f0324SBarry Smith printf("%s ",hostname); 1021df1832dSBarry Smith } 103436f0324SBarry Smith printf("\n"); 1041df1832dSBarry Smith } else { 1051df1832dSBarry Smith MPI_Send(hostname,MPI_MAX_PROCESSOR_NAME,MPI_CHAR,0,0,MPI_COMM_WORLD); 106d3ae85c4SBarry Smith } 107*b7250d5dSSatish Balay ierr = MPI_Barrier(MPI_COMM_WORLD); 108d3ae85c4SBarry Smith 109d3ae85c4SBarry Smith /* --- SETUP --- determine precision and check timing --- */ 110d3ae85c4SBarry Smith 111d3ae85c4SBarry Smith if (!rank) { 112d3ae85c4SBarry Smith /*printf(HLINE); 113d3ae85c4SBarry Smith printf("Array size = %d, Offset = %d\n" , N, OFFSET); 114d3ae85c4SBarry Smith printf("Total memory required = %.1f MB.\n", (3 * N * BytesPerWord) / 1048576.0); 115d3ae85c4SBarry Smith printf("Each test is run %d times, but only\n", NTIMES); 116d3ae85c4SBarry Smith printf("the *best* time for each is used.\n"); 117d3ae85c4SBarry Smith printf(HLINE); */ 118d3ae85c4SBarry Smith } 119d3ae85c4SBarry Smith 120d3ae85c4SBarry Smith /* Get initial value for system clock. */ 121d3ae85c4SBarry Smith 122d3ae85c4SBarry Smith /* a = malloc(N*sizeof(double)); 123d3ae85c4SBarry Smith b = malloc(N*sizeof(double)); 124d3ae85c4SBarry Smith c = malloc(N*sizeof(double));*/ 125d3ae85c4SBarry Smith for (j=0; j<N; j++) { 126d3ae85c4SBarry Smith a[j] = 1.0; 127d3ae85c4SBarry Smith b[j] = 2.0; 128d3ae85c4SBarry Smith c[j] = 0.0; 129d3ae85c4SBarry Smith } 130d3ae85c4SBarry Smith 131d3ae85c4SBarry Smith if (!rank) { 132d3ae85c4SBarry Smith if ((quantum = checktick()) >= 1) ; /* printf("Your clock granularity/precision appears to be %d microseconds.\n", quantum); */ 133d3ae85c4SBarry Smith else ; /* printf("Your clock granularity appears to be less than one microsecond.\n");*/ 134d3ae85c4SBarry Smith } 135d3ae85c4SBarry Smith 13619623ac0SBarry Smith t = MPI_Wtime(); 137d3ae85c4SBarry Smith for (j = 0; j < N; j++) a[j] = 2.0E0 * a[j]; 13819623ac0SBarry Smith t = 1.0E6 * (MPI_Wtime() - t); 139d3ae85c4SBarry Smith 140d3ae85c4SBarry Smith if (!rank) { 141d3ae85c4SBarry Smith /* printf("Each test below will take on the order of %d microseconds.\n", (int) t); 142d3ae85c4SBarry Smith printf(" (= %d clock ticks)\n", (int) (t/quantum)); 143d3ae85c4SBarry Smith printf("Increase the size of the arrays if this shows that\n"); 144d3ae85c4SBarry Smith printf("you are not getting at least 20 clock ticks per test.\n"); 145d3ae85c4SBarry Smith printf(HLINE);*/ 146d3ae85c4SBarry Smith } 147d3ae85c4SBarry Smith 148d3ae85c4SBarry Smith 149d3ae85c4SBarry Smith /* --- MAIN LOOP --- repeat test cases NTIMES times --- */ 150d3ae85c4SBarry Smith 151d3ae85c4SBarry Smith scalar = 3.0; 152d3ae85c4SBarry Smith for (k=0; k<NTIMES; k++) 153d3ae85c4SBarry Smith { 154*b7250d5dSSatish Balay ierr = MPI_Barrier(MPI_COMM_WORLD); 15519623ac0SBarry Smith times[0][k] = MPI_Wtime(); 156d3ae85c4SBarry Smith /* should all these barriers be pulled outside of the time call? */ 157*b7250d5dSSatish Balay ierr = MPI_Barrier(MPI_COMM_WORLD); 158d3ae85c4SBarry Smith for (j=0; j<N; j++) c[j] = a[j]; 159*b7250d5dSSatish Balay ierr = MPI_Barrier(MPI_COMM_WORLD); 16019623ac0SBarry Smith times[0][k] = MPI_Wtime() - times[0][k]; 161d3ae85c4SBarry Smith 16219623ac0SBarry Smith times[1][k] = MPI_Wtime(); 163*b7250d5dSSatish Balay ierr = MPI_Barrier(MPI_COMM_WORLD); 164d3ae85c4SBarry Smith for (j=0; j<N; j++) b[j] = scalar*c[j]; 165*b7250d5dSSatish Balay ierr = MPI_Barrier(MPI_COMM_WORLD); 16619623ac0SBarry Smith times[1][k] = MPI_Wtime() - times[1][k]; 167d3ae85c4SBarry Smith 16819623ac0SBarry Smith times[2][k] = MPI_Wtime(); 169*b7250d5dSSatish Balay ierr = MPI_Barrier(MPI_COMM_WORLD); 170d3ae85c4SBarry Smith for (j=0; j<N; j++) c[j] = a[j]+b[j]; 171*b7250d5dSSatish Balay ierr = MPI_Barrier(MPI_COMM_WORLD); 17219623ac0SBarry Smith times[2][k] = MPI_Wtime() - times[2][k]; 173d3ae85c4SBarry Smith 17419623ac0SBarry Smith times[3][k] = MPI_Wtime(); 175*b7250d5dSSatish Balay ierr = MPI_Barrier(MPI_COMM_WORLD); 176d3ae85c4SBarry Smith for (j=0; j<N; j++) a[j] = b[j]+scalar*c[j]; 177*b7250d5dSSatish Balay ierr = MPI_Barrier(MPI_COMM_WORLD); 17819623ac0SBarry Smith times[3][k] = MPI_Wtime() - times[3][k]; 179d3ae85c4SBarry Smith } 180d3ae85c4SBarry Smith 181d3ae85c4SBarry Smith /* --- SUMMARY --- */ 182d3ae85c4SBarry Smith 183d3ae85c4SBarry Smith for (k=0; k<NTIMES; k++) 184d3ae85c4SBarry Smith for (j=0; j<4; j++) mintime[j] = MIN(mintime[j], times[j][k]); 185d3ae85c4SBarry Smith 186d3ae85c4SBarry Smith for (j=0; j<4; j++) irate[j] = 1.0E-06 * bytes[j]/mintime[j]; 187*b7250d5dSSatish Balay ierr = MPI_Reduce(irate,rate,4,MPI_DOUBLE,MPI_SUM,0,MPI_COMM_WORLD); 188*b7250d5dSSatish Balay if (ierr) printf("Error calling MPI\n"); 189d3ae85c4SBarry Smith 190d3ae85c4SBarry Smith if (!rank) { 191436f0324SBarry Smith printf("%s %11.4f Rate (MB/s) \n", label[3],rate[3]); 192436f0324SBarry Smith /* for (j=0; j<4; j++) printf("%s%11.4f\n", label[j],rate[j]);*/ 193d3ae85c4SBarry Smith } 194d3ae85c4SBarry Smith MPI_Finalize(); 195d3ae85c4SBarry Smith return 0; 196d3ae85c4SBarry Smith } 197d3ae85c4SBarry Smith 198d3ae85c4SBarry Smith # define M 20 199d3ae85c4SBarry Smith 200d1d3a73cSBarry Smith int checktick(void) 201d3ae85c4SBarry Smith { 202d3ae85c4SBarry Smith int i, minDelta, Delta; 203d3ae85c4SBarry Smith double t1, t2, timesfound[M]; 204d3ae85c4SBarry Smith 205d3ae85c4SBarry Smith /* Collect a sequence of M unique time values from the system. */ 206d3ae85c4SBarry Smith 207d3ae85c4SBarry Smith for (i = 0; i < M; i++) { 20819623ac0SBarry Smith t1 = MPI_Wtime(); 20919623ac0SBarry Smith while (((t2=MPI_Wtime()) - t1) < 1.0E-6) ; 210d3ae85c4SBarry Smith timesfound[i] = t1 = t2; 211d3ae85c4SBarry Smith } 212d3ae85c4SBarry Smith 213d3ae85c4SBarry Smith /* 214d3ae85c4SBarry Smith * Determine the minimum difference between these M values. 215d3ae85c4SBarry Smith * This result will be our estimate (in microseconds) for the 216d3ae85c4SBarry Smith * clock granularity. 217d3ae85c4SBarry Smith */ 218d3ae85c4SBarry Smith 219d3ae85c4SBarry Smith minDelta = 1000000; 220d3ae85c4SBarry Smith for (i = 1; i < M; i++) { 221d3ae85c4SBarry Smith Delta = (int)(1.0E6 * (timesfound[i]-timesfound[i-1])); 222d3ae85c4SBarry Smith minDelta = MIN(minDelta, MAX(Delta,0)); 223d3ae85c4SBarry Smith } 224d3ae85c4SBarry Smith 225d3ae85c4SBarry Smith return(minDelta); 226d3ae85c4SBarry Smith } 227d3ae85c4SBarry Smith 228