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 76*e109280bSBarry 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; 86d3ae85c4SBarry Smith 87d3ae85c4SBarry Smith MPI_Init(&argc,&args); 88d3ae85c4SBarry Smith MPI_Comm_rank(MPI_COMM_WORLD,&rank); 89d3ae85c4SBarry Smith MPI_Comm_size(MPI_COMM_WORLD,&size); 90436f0324SBarry Smith if (!rank) printf("Number of MPI processes %d ",size); 91d3ae85c4SBarry Smith 926b58a888SBarry Smith for (j=0; j<MPI_MAX_PROCESSOR_NAME; j++) { 936b58a888SBarry Smith hostname[j] = 0; 946b58a888SBarry Smith } 95d3ae85c4SBarry Smith MPI_Get_processor_name(hostname,&resultlen); 961df1832dSBarry Smith if (!rank) { 97436f0324SBarry Smith printf("Processor names %s ",hostname); 981df1832dSBarry Smith for (j=1; j<size; j++) { 991df1832dSBarry Smith MPI_Recv(hostname,MPI_MAX_PROCESSOR_NAME,MPI_CHAR,j,0,MPI_COMM_WORLD,&status); 100436f0324SBarry Smith printf("%s ",hostname); 1011df1832dSBarry Smith } 102436f0324SBarry Smith printf("\n"); 1031df1832dSBarry Smith } else { 1041df1832dSBarry Smith MPI_Send(hostname,MPI_MAX_PROCESSOR_NAME,MPI_CHAR,0,0,MPI_COMM_WORLD); 105d3ae85c4SBarry Smith } 106d3ae85c4SBarry Smith MPI_Barrier(MPI_COMM_WORLD); 107d3ae85c4SBarry Smith 108d3ae85c4SBarry Smith /* --- SETUP --- determine precision and check timing --- */ 109d3ae85c4SBarry Smith 110d3ae85c4SBarry Smith if (!rank) { 111d3ae85c4SBarry Smith /*printf(HLINE); 112d3ae85c4SBarry Smith printf("Array size = %d, Offset = %d\n" , N, OFFSET); 113d3ae85c4SBarry Smith printf("Total memory required = %.1f MB.\n", (3 * N * BytesPerWord) / 1048576.0); 114d3ae85c4SBarry Smith printf("Each test is run %d times, but only\n", NTIMES); 115d3ae85c4SBarry Smith printf("the *best* time for each is used.\n"); 116d3ae85c4SBarry Smith printf(HLINE); */ 117d3ae85c4SBarry Smith } 118d3ae85c4SBarry Smith 119d3ae85c4SBarry Smith /* Get initial value for system clock. */ 120d3ae85c4SBarry Smith 121d3ae85c4SBarry Smith /* a = malloc(N*sizeof(double)); 122d3ae85c4SBarry Smith b = malloc(N*sizeof(double)); 123d3ae85c4SBarry Smith c = malloc(N*sizeof(double));*/ 124d3ae85c4SBarry Smith for (j=0; j<N; j++) { 125d3ae85c4SBarry Smith a[j] = 1.0; 126d3ae85c4SBarry Smith b[j] = 2.0; 127d3ae85c4SBarry Smith c[j] = 0.0; 128d3ae85c4SBarry Smith } 129d3ae85c4SBarry Smith 130d3ae85c4SBarry Smith if (!rank) { 131d3ae85c4SBarry Smith if ((quantum = checktick()) >= 1) ; /* printf("Your clock granularity/precision appears to be %d microseconds.\n", quantum); */ 132d3ae85c4SBarry Smith else ; /* printf("Your clock granularity appears to be less than one microsecond.\n");*/ 133d3ae85c4SBarry Smith } 134d3ae85c4SBarry Smith 13519623ac0SBarry Smith t = MPI_Wtime(); 136d3ae85c4SBarry Smith for (j = 0; j < N; j++) a[j] = 2.0E0 * a[j]; 13719623ac0SBarry Smith t = 1.0E6 * (MPI_Wtime() - t); 138d3ae85c4SBarry Smith 139d3ae85c4SBarry Smith if (!rank) { 140d3ae85c4SBarry Smith /* printf("Each test below will take on the order of %d microseconds.\n", (int) t); 141d3ae85c4SBarry Smith printf(" (= %d clock ticks)\n", (int) (t/quantum)); 142d3ae85c4SBarry Smith printf("Increase the size of the arrays if this shows that\n"); 143d3ae85c4SBarry Smith printf("you are not getting at least 20 clock ticks per test.\n"); 144d3ae85c4SBarry Smith printf(HLINE);*/ 145d3ae85c4SBarry Smith } 146d3ae85c4SBarry Smith 147d3ae85c4SBarry Smith 148d3ae85c4SBarry Smith /* --- MAIN LOOP --- repeat test cases NTIMES times --- */ 149d3ae85c4SBarry Smith 150d3ae85c4SBarry Smith scalar = 3.0; 151d3ae85c4SBarry Smith for (k=0; k<NTIMES; k++) 152d3ae85c4SBarry Smith { 153d3ae85c4SBarry Smith MPI_Barrier(MPI_COMM_WORLD); 15419623ac0SBarry Smith times[0][k] = MPI_Wtime(); 155d3ae85c4SBarry Smith /* should all these barriers be pulled outside of the time call? */ 156d3ae85c4SBarry Smith MPI_Barrier(MPI_COMM_WORLD); 157d3ae85c4SBarry Smith for (j=0; j<N; j++) c[j] = a[j]; 158d3ae85c4SBarry Smith MPI_Barrier(MPI_COMM_WORLD); 15919623ac0SBarry Smith times[0][k] = MPI_Wtime() - times[0][k]; 160d3ae85c4SBarry Smith 16119623ac0SBarry Smith times[1][k] = MPI_Wtime(); 162d3ae85c4SBarry Smith MPI_Barrier(MPI_COMM_WORLD); 163d3ae85c4SBarry Smith for (j=0; j<N; j++) b[j] = scalar*c[j]; 164d3ae85c4SBarry Smith MPI_Barrier(MPI_COMM_WORLD); 16519623ac0SBarry Smith times[1][k] = MPI_Wtime() - times[1][k]; 166d3ae85c4SBarry Smith 16719623ac0SBarry Smith times[2][k] = MPI_Wtime(); 168d3ae85c4SBarry Smith MPI_Barrier(MPI_COMM_WORLD); 169d3ae85c4SBarry Smith for (j=0; j<N; j++) c[j] = a[j]+b[j]; 170d3ae85c4SBarry Smith MPI_Barrier(MPI_COMM_WORLD); 17119623ac0SBarry Smith times[2][k] = MPI_Wtime() - times[2][k]; 172d3ae85c4SBarry Smith 17319623ac0SBarry Smith times[3][k] = MPI_Wtime(); 174d3ae85c4SBarry Smith MPI_Barrier(MPI_COMM_WORLD); 175d3ae85c4SBarry Smith for (j=0; j<N; j++) a[j] = b[j]+scalar*c[j]; 176d3ae85c4SBarry Smith MPI_Barrier(MPI_COMM_WORLD); 17719623ac0SBarry Smith times[3][k] = MPI_Wtime() - times[3][k]; 178d3ae85c4SBarry Smith } 179d3ae85c4SBarry Smith 180d3ae85c4SBarry Smith /* --- SUMMARY --- */ 181d3ae85c4SBarry Smith 182d3ae85c4SBarry Smith for (k=0; k<NTIMES; k++) 183d3ae85c4SBarry Smith for (j=0; j<4; j++) mintime[j] = MIN(mintime[j], times[j][k]); 184d3ae85c4SBarry Smith 185d3ae85c4SBarry Smith for (j=0; j<4; j++) irate[j] = 1.0E-06 * bytes[j]/mintime[j]; 186d3ae85c4SBarry Smith MPI_Reduce(irate,rate,4,MPI_DOUBLE,MPI_SUM,0,MPI_COMM_WORLD); 187d3ae85c4SBarry Smith 188d3ae85c4SBarry Smith if (!rank) { 189436f0324SBarry Smith printf("%s %11.4f Rate (MB/s) \n", label[3],rate[3]); 190436f0324SBarry Smith /* for (j=0; j<4; j++) printf("%s%11.4f\n", label[j],rate[j]);*/ 191d3ae85c4SBarry Smith } 192d3ae85c4SBarry Smith MPI_Finalize(); 193d3ae85c4SBarry Smith return 0; 194d3ae85c4SBarry Smith } 195d3ae85c4SBarry Smith 196d3ae85c4SBarry Smith # define M 20 197d3ae85c4SBarry Smith 198d1d3a73cSBarry Smith int checktick(void) 199d3ae85c4SBarry Smith { 200d3ae85c4SBarry Smith int i, minDelta, Delta; 201d3ae85c4SBarry Smith double t1, t2, timesfound[M]; 202d3ae85c4SBarry Smith 203d3ae85c4SBarry Smith /* Collect a sequence of M unique time values from the system. */ 204d3ae85c4SBarry Smith 205d3ae85c4SBarry Smith for (i = 0; i < M; i++) { 20619623ac0SBarry Smith t1 = MPI_Wtime(); 20719623ac0SBarry Smith while (((t2=MPI_Wtime()) - t1) < 1.0E-6) ; 208d3ae85c4SBarry Smith timesfound[i] = t1 = t2; 209d3ae85c4SBarry Smith } 210d3ae85c4SBarry Smith 211d3ae85c4SBarry Smith /* 212d3ae85c4SBarry Smith * Determine the minimum difference between these M values. 213d3ae85c4SBarry Smith * This result will be our estimate (in microseconds) for the 214d3ae85c4SBarry Smith * clock granularity. 215d3ae85c4SBarry Smith */ 216d3ae85c4SBarry Smith 217d3ae85c4SBarry Smith minDelta = 1000000; 218d3ae85c4SBarry Smith for (i = 1; i < M; i++) { 219d3ae85c4SBarry Smith Delta = (int)(1.0E6 * (timesfound[i]-timesfound[i-1])); 220d3ae85c4SBarry Smith minDelta = MIN(minDelta, MAX(Delta,0)); 221d3ae85c4SBarry Smith } 222d3ae85c4SBarry Smith 223d3ae85c4SBarry Smith return(minDelta); 224d3ae85c4SBarry Smith } 225d3ae85c4SBarry Smith 226