159599516SKenneth E. Jansen /* 259599516SKenneth E. Jansen * 359599516SKenneth E. Jansen * This is the SyncIO library that uses MPI-IO collective functions to 459599516SKenneth E. Jansen * implement a flexible I/O checkpoint solution for a large number of 559599516SKenneth E. Jansen * processors. 659599516SKenneth E. Jansen * 759599516SKenneth E. Jansen * Previous developer: Ning Liu (liun2@cs.rpi.edu) 859599516SKenneth E. Jansen * Jing Fu (fuj@cs.rpi.edu) 959599516SKenneth E. Jansen * Current developers: Michel Rasquin (Michel.Rasquin@colorado.edu), 1059599516SKenneth E. Jansen * Ben Matthews (benjamin.a.matthews@colorado.edu) 1159599516SKenneth E. Jansen * 1259599516SKenneth E. Jansen */ 1359599516SKenneth E. Jansen 1459599516SKenneth E. Jansen #include <map> 1559599516SKenneth E. Jansen #include <vector> 1659599516SKenneth E. Jansen #include <string> 17*a746c838SCameron Smith #include <cstdarg> 1859599516SKenneth E. Jansen #include <string.h> 1959599516SKenneth E. Jansen #include <ctype.h> 2059599516SKenneth E. Jansen #include <stdlib.h> 2159599516SKenneth E. Jansen #include <stdio.h> 2259599516SKenneth E. Jansen #include <math.h> 23d3337298SCameron Smith #include <sstream> 2459599516SKenneth E. Jansen #include "phastaIO.h" 2559599516SKenneth E. Jansen #include "mpi.h" 2659599516SKenneth E. Jansen #include "phiotmrc.h" 2797a07b0aSCameron Smith #include <assert.h> 2859599516SKenneth E. Jansen 2959599516SKenneth E. Jansen #define VERSION_INFO_HEADER_SIZE 8192 3059599516SKenneth E. Jansen #define DB_HEADER_SIZE 1024 3159599516SKenneth E. Jansen #define ONE_MEGABYTE 1048576 3259599516SKenneth E. Jansen #define TWO_MEGABYTE 2097152 3359599516SKenneth E. Jansen #define ENDIAN_TEST_NUMBER 12180 // Troy's Zip Code!! 3459599516SKenneth E. Jansen #define MAX_PHASTA_FILES 64 3559599516SKenneth E. Jansen #define MAX_PHASTA_FILE_NAME_LENGTH 1024 3659599516SKenneth E. Jansen #define MAX_FIELDS_NUMBER ((VERSION_INFO_HEADER_SIZE/MAX_FIELDS_NAME_LENGTH)-4) // The meta data include - MPI_IO_Tag, nFields, nFields*names of the fields, nppf 3759599516SKenneth E. Jansen // -3 for MPI_IO_Tag, nFields and nppf, -4 for extra security (former nFiles) 3859599516SKenneth E. Jansen #define MAX_FIELDS_NAME_LENGTH 128 3959599516SKenneth E. Jansen #define DefaultMHSize (4*ONE_MEGABYTE) 4059599516SKenneth E. Jansen //#define DefaultMHSize (8350) //For test 4159599516SKenneth E. Jansen #define LATEST_WRITE_VERSION 1 4259599516SKenneth E. Jansen #define inv1024sq 953.674316406e-9 // = 1/1024/1024 4359599516SKenneth E. Jansen int MasterHeaderSize = -1; 4459599516SKenneth E. Jansen 4559599516SKenneth E. Jansen bool PRINT_PERF = false; // default print no perf results 4659599516SKenneth E. Jansen int irank = -1; // global rank, should never be manually manipulated 4759599516SKenneth E. Jansen int mysize = -1; 4859599516SKenneth E. Jansen 4959599516SKenneth E. Jansen // Static variables are bad but used here to store the subcommunicator and associated variables 5059599516SKenneth E. Jansen // Prevent MPI_Comm_split to be called more than once, especially on BGQ with the V1R2M1 driver (leak detected in MPI_Comm_split - IBM working on it) 5159599516SKenneth E. Jansen static int s_assign_local_comm = 0; 5259599516SKenneth E. Jansen static MPI_Comm s_local_comm; 5359599516SKenneth E. Jansen static int s_local_size = -1; 5459599516SKenneth E. Jansen static int s_local_rank = -1; 5559599516SKenneth E. Jansen 5659599516SKenneth E. Jansen // the following defines are for debug printf 5759599516SKenneth E. Jansen #define PHASTAIO_DEBUG 0 //default to not print any debugging info 5859599516SKenneth E. Jansen 59fe03b87fSCameron Smith void phprintf(const char* fmt, ...) { 60be3da47bSCameron Smith (void)fmt; 6159599516SKenneth E. Jansen #if PHASTAIO_DEBUG 62fe03b87fSCameron Smith char format[1024]; 63fe03b87fSCameron Smith snprintf(format, sizeof(format), "phastaIO debug: %s", fmt); 64fe03b87fSCameron Smith va_list ap; 65fe03b87fSCameron Smith va_start(ap,fmt); 66*a746c838SCameron Smith vprintf(format,ap); 67fe03b87fSCameron Smith va_end(ap); 6859599516SKenneth E. Jansen #endif 69fe03b87fSCameron Smith } 70fe03b87fSCameron Smith 71fe03b87fSCameron Smith void phprintf_0(const char* fmt, ...) { 72be3da47bSCameron Smith (void)fmt; 73fe03b87fSCameron Smith #if PHASTAIO_DEBUG 74fe03b87fSCameron Smith int rank = 0; 75fe03b87fSCameron Smith MPI_Comm_rank(MPI_COMM_WORLD, &rank); 76fe03b87fSCameron Smith if(rank == 0){ 77fe03b87fSCameron Smith char format[1024]; 78fe03b87fSCameron Smith snprintf(format, sizeof(format), "phastaIO debug: irank=0 %s", fmt); 79fe03b87fSCameron Smith va_list ap; 80*a746c838SCameron Smith va_start(ap,fmt); 81fe03b87fSCameron Smith vprintf(format, ap); 82fe03b87fSCameron Smith va_end(ap); 83fe03b87fSCameron Smith } 84fe03b87fSCameron Smith #endif 85fe03b87fSCameron Smith } 8659599516SKenneth E. Jansen 8759599516SKenneth E. Jansen enum PhastaIO_Errors 8859599516SKenneth E. Jansen { 8959599516SKenneth E. Jansen MAX_PHASTA_FILES_EXCEEDED = -1, 9059599516SKenneth E. Jansen UNABLE_TO_OPEN_FILE = -2, 9159599516SKenneth E. Jansen NOT_A_MPI_FILE = -3, 9259599516SKenneth E. Jansen GPID_EXCEEDED = -4, 9310d56689SCameron Smith DATA_TYPE_ILLEGAL = -5 9459599516SKenneth E. Jansen }; 9559599516SKenneth E. Jansen 9659599516SKenneth E. Jansen using namespace std; 9759599516SKenneth E. Jansen 9859599516SKenneth E. Jansen namespace{ 9959599516SKenneth E. Jansen 100961a4ff6SCameron Smith map<int, std::string> LastHeaderKey; 10159599516SKenneth E. Jansen vector< FILE* > fileArray; 10259599516SKenneth E. Jansen vector< bool > byte_order; 10359599516SKenneth E. Jansen vector< int > header_type; 10459599516SKenneth E. Jansen int DataSize=0; 10559599516SKenneth E. Jansen bool LastHeaderNotFound = false; 10659599516SKenneth E. Jansen bool Wrong_Endian = false ; 10759599516SKenneth E. Jansen bool Strict_Error = false ; 10859599516SKenneth E. Jansen bool binary_format = true; 10959599516SKenneth E. Jansen 11059599516SKenneth E. Jansen /***********************************************************************/ 11159599516SKenneth E. Jansen /***************** NEW PHASTA IO CODE STARTS HERE **********************/ 11259599516SKenneth E. Jansen /***********************************************************************/ 11359599516SKenneth E. Jansen 11459599516SKenneth E. Jansen typedef struct 11559599516SKenneth E. Jansen { 11659599516SKenneth E. Jansen char filename[MAX_PHASTA_FILE_NAME_LENGTH]; /* defafults to 1024 */ 1172dd307a1SCameron Smith unsigned long my_offset; 1182dd307a1SCameron Smith unsigned long next_start_address; 1192dd307a1SCameron Smith unsigned long **my_offset_table; 1202dd307a1SCameron Smith unsigned long **my_read_table; 12159599516SKenneth E. Jansen 12259599516SKenneth E. Jansen double * double_chunk; 12359599516SKenneth E. Jansen double * read_double_chunk; 12459599516SKenneth E. Jansen 12559599516SKenneth E. Jansen int field_count; 12659599516SKenneth E. Jansen int part_count; 12759599516SKenneth E. Jansen int read_field_count; 12859599516SKenneth E. Jansen int read_part_count; 12959599516SKenneth E. Jansen int GPid; 13059599516SKenneth E. Jansen int start_id; 13159599516SKenneth E. Jansen 13259599516SKenneth E. Jansen int mhsize; 13359599516SKenneth E. Jansen 13459599516SKenneth E. Jansen int myrank; 13559599516SKenneth E. Jansen int numprocs; 13659599516SKenneth E. Jansen int local_myrank; 13759599516SKenneth E. Jansen int local_numprocs; 13859599516SKenneth E. Jansen 13959599516SKenneth E. Jansen int nppp; 14059599516SKenneth E. Jansen int nPPF; 14159599516SKenneth E. Jansen int nFiles; 14259599516SKenneth E. Jansen int nFields; 14359599516SKenneth E. Jansen 14459599516SKenneth E. Jansen int * int_chunk; 14559599516SKenneth E. Jansen int * read_int_chunk; 14659599516SKenneth E. Jansen 14759599516SKenneth E. Jansen int Wrong_Endian; /* default to false */ 14859599516SKenneth E. Jansen char * master_header; 14959599516SKenneth E. Jansen MPI_File file_handle; 15059599516SKenneth E. Jansen MPI_Comm local_comm; 15159599516SKenneth E. Jansen } phastaio_file_t; 15259599516SKenneth E. Jansen 15359599516SKenneth E. Jansen typedef struct 15459599516SKenneth E. Jansen { 15559599516SKenneth E. Jansen int nppf, nfields; 15659599516SKenneth E. Jansen char * masterHeader; 15759599516SKenneth E. Jansen }serial_file; 15859599516SKenneth E. Jansen 15959599516SKenneth E. Jansen serial_file *SerialFile; 16059599516SKenneth E. Jansen phastaio_file_t *PhastaIOActiveFiles[MAX_PHASTA_FILES]; 16159599516SKenneth E. Jansen int PhastaIONextActiveIndex = 0; /* indicates next index to allocate */ 16259599516SKenneth E. Jansen 16359599516SKenneth E. Jansen // the caller has the responsibility to delete the returned string 16459599516SKenneth E. Jansen // TODO: StringStipper("nbc value? ") returns NULL? 165103be424SCameron Smith char* StringStripper( const char istring[] ) { 16659599516SKenneth E. Jansen int length = strlen( istring ); 16759599516SKenneth E. Jansen char* dest = (char *)malloc( length + 1 ); 16859599516SKenneth E. Jansen strcpy( dest, istring ); 16959599516SKenneth E. Jansen dest[ length ] = '\0'; 17059599516SKenneth E. Jansen if ( char* p = strpbrk( dest, " ") ) 17159599516SKenneth E. Jansen *p = '\0'; 17259599516SKenneth E. Jansen return dest; 17359599516SKenneth E. Jansen } 17459599516SKenneth E. Jansen 175103be424SCameron Smith inline int cscompare( const char teststring[], const char targetstring[] ) { 17659599516SKenneth E. Jansen char* s1 = const_cast<char*>(teststring); 17759599516SKenneth E. Jansen char* s2 = const_cast<char*>(targetstring); 17859599516SKenneth E. Jansen 17959599516SKenneth E. Jansen while( *s1 == ' ') s1++; 18059599516SKenneth E. Jansen while( *s2 == ' ') s2++; 18159599516SKenneth E. Jansen while( ( *s1 ) 18259599516SKenneth E. Jansen && ( *s2 ) 18359599516SKenneth E. Jansen && ( *s2 != '?') 18459599516SKenneth E. Jansen && ( tolower( *s1 )==tolower( *s2 ) ) ) { 18559599516SKenneth E. Jansen s1++; 18659599516SKenneth E. Jansen s2++; 18759599516SKenneth E. Jansen while( *s1 == ' ') s1++; 18859599516SKenneth E. Jansen while( *s2 == ' ') s2++; 18959599516SKenneth E. Jansen } 19059599516SKenneth E. Jansen if ( !( *s1 ) || ( *s1 == '?') ) return 1; 19159599516SKenneth E. Jansen else return 0; 19259599516SKenneth E. Jansen } 19359599516SKenneth E. Jansen 194103be424SCameron Smith inline void isBinary( const char iotype[] ) { 19559599516SKenneth E. Jansen char* fname = StringStripper( iotype ); 19659599516SKenneth E. Jansen if ( cscompare( fname, "binary" ) ) binary_format = true; 19759599516SKenneth E. Jansen else binary_format = false; 19859599516SKenneth E. Jansen free (fname); 19959599516SKenneth E. Jansen 20059599516SKenneth E. Jansen } 20159599516SKenneth E. Jansen 202103be424SCameron Smith inline size_t typeSize( const char typestring[] ) { 20359599516SKenneth E. Jansen char* ts1 = StringStripper( typestring ); 20459599516SKenneth E. Jansen if ( cscompare( "integer", ts1 ) ) { 20559599516SKenneth E. Jansen free (ts1); 20659599516SKenneth E. Jansen return sizeof(int); 20759599516SKenneth E. Jansen } else if ( cscompare( "double", ts1 ) ) { 20859599516SKenneth E. Jansen free (ts1); 20959599516SKenneth E. Jansen return sizeof( double ); 21059599516SKenneth E. Jansen } else { 21159599516SKenneth E. Jansen free (ts1); 21259599516SKenneth E. Jansen fprintf(stderr,"unknown type : %s\n",ts1); 21359599516SKenneth E. Jansen return 0; 21459599516SKenneth E. Jansen } 21559599516SKenneth E. Jansen } 21659599516SKenneth E. Jansen 217103be424SCameron Smith int readHeader( 218103be424SCameron Smith FILE* fileObject, 21959599516SKenneth E. Jansen const char phrase[], 22059599516SKenneth E. Jansen int* params, 22159599516SKenneth E. Jansen int expect ) { 22259599516SKenneth E. Jansen char* text_header; 22359599516SKenneth E. Jansen char* token; 22497a07b0aSCameron Smith char Line[1024] = "\0"; 22559599516SKenneth E. Jansen char junk; 22659599516SKenneth E. Jansen bool FOUND = false ; 22759599516SKenneth E. Jansen int real_length; 22859599516SKenneth E. Jansen int skip_size, integer_value; 22959599516SKenneth E. Jansen int rewind_count=0; 23059599516SKenneth E. Jansen 23159599516SKenneth E. Jansen if( !fgets( Line, 1024, fileObject ) && feof( fileObject ) ) { 23259599516SKenneth E. Jansen rewind( fileObject ); 23359599516SKenneth E. Jansen clearerr( fileObject ); 23459599516SKenneth E. Jansen rewind_count++; 23559599516SKenneth E. Jansen fgets( Line, 1024, fileObject ); 23659599516SKenneth E. Jansen } 23759599516SKenneth E. Jansen 23859599516SKenneth E. Jansen while( !FOUND && ( rewind_count < 2 ) ) { 23959599516SKenneth E. Jansen if ( ( Line[0] != '\n' ) && ( real_length = strcspn( Line, "#" )) ) { 24059599516SKenneth E. Jansen text_header = (char *)malloc( real_length + 1 ); 24159599516SKenneth E. Jansen strncpy( text_header, Line, real_length ); 24259599516SKenneth E. Jansen text_header[ real_length ] =static_cast<char>(NULL); 24359599516SKenneth E. Jansen token = strtok ( text_header, ":" ); 24497a07b0aSCameron Smith assert(token); 24597a07b0aSCameron Smith if( cscompare( phrase , token ) ) { 24659599516SKenneth E. Jansen FOUND = true ; 24759599516SKenneth E. Jansen token = strtok( NULL, " ,;<>" ); 24897a07b0aSCameron Smith assert(token); 24959599516SKenneth E. Jansen skip_size = atoi( token ); 25059599516SKenneth E. Jansen int i; 25159599516SKenneth E. Jansen for( i=0; i < expect && ( token = strtok( NULL," ,;<>") ); i++) { 25297a07b0aSCameron Smith assert(token); 25359599516SKenneth E. Jansen params[i] = atoi( token ); 25459599516SKenneth E. Jansen } 25559599516SKenneth E. Jansen if ( i < expect ) { 256103be424SCameron Smith fprintf(stderr, 257103be424SCameron Smith "Aloha Expected # of ints not found for: %s\n",phrase ); 25859599516SKenneth E. Jansen } 25959599516SKenneth E. Jansen } else if ( cscompare(token,"byteorder magic number") ) { 26059599516SKenneth E. Jansen if ( binary_format ) { 26159599516SKenneth E. Jansen fread((void*)&integer_value,sizeof(int),1,fileObject); 26259599516SKenneth E. Jansen fread( &junk, sizeof(char), 1 , fileObject ); 26359599516SKenneth E. Jansen if ( 362436 != integer_value ) Wrong_Endian = true; 26459599516SKenneth E. Jansen } else{ 26559599516SKenneth E. Jansen fscanf(fileObject, "%d\n", &integer_value ); 26659599516SKenneth E. Jansen } 26759599516SKenneth E. Jansen } else { 26859599516SKenneth E. Jansen /* some other header, so just skip over */ 26959599516SKenneth E. Jansen token = strtok( NULL, " ,;<>" ); 27097a07b0aSCameron Smith assert(token); 27159599516SKenneth E. Jansen skip_size = atoi( token ); 27259599516SKenneth E. Jansen if ( binary_format) 27359599516SKenneth E. Jansen fseek( fileObject, skip_size, SEEK_CUR ); 27459599516SKenneth E. Jansen else 27559599516SKenneth E. Jansen for( int gama=0; gama < skip_size; gama++ ) 27659599516SKenneth E. Jansen fgets( Line, 1024, fileObject ); 27759599516SKenneth E. Jansen } 27859599516SKenneth E. Jansen free (text_header); 27959599516SKenneth E. Jansen } // end of if before while loop 28059599516SKenneth E. Jansen 28159599516SKenneth E. Jansen if ( !FOUND ) 28259599516SKenneth E. Jansen if( !fgets( Line, 1024, fileObject ) && feof( fileObject ) ) { 28359599516SKenneth E. Jansen rewind( fileObject ); 28459599516SKenneth E. Jansen clearerr( fileObject ); 28559599516SKenneth E. Jansen rewind_count++; 28659599516SKenneth E. Jansen fgets( Line, 1024, fileObject ); 28759599516SKenneth E. Jansen } 28859599516SKenneth E. Jansen } 28959599516SKenneth E. Jansen 29059599516SKenneth E. Jansen if ( !FOUND ) { 29159599516SKenneth E. Jansen //fprintf(stderr, "Error: Could not find: %s\n", phrase); 29259599516SKenneth E. Jansen if(irank == 0) printf("WARNING: Could not find: %s\n", phrase); 29359599516SKenneth E. Jansen return 1; 29459599516SKenneth E. Jansen } 29559599516SKenneth E. Jansen return 0; 29659599516SKenneth E. Jansen } 29759599516SKenneth E. Jansen 29859599516SKenneth E. Jansen } // end unnamed namespace 29959599516SKenneth E. Jansen 30059599516SKenneth E. Jansen 30159599516SKenneth E. Jansen // begin of publicly visible functions 30259599516SKenneth E. Jansen 30359599516SKenneth E. Jansen /** 30459599516SKenneth E. Jansen * This function takes a long long pointer and assign (start) phiotmrc value to it 30559599516SKenneth E. Jansen */ 30659599516SKenneth E. Jansen void startTimer(double* start) { 30759599516SKenneth E. Jansen if( !PRINT_PERF ) return; 30859599516SKenneth E. Jansen MPI_Barrier(MPI_COMM_WORLD); 30959599516SKenneth E. Jansen *start = phiotmrc(); 31059599516SKenneth E. Jansen } 31159599516SKenneth E. Jansen 31259599516SKenneth E. Jansen /** 31359599516SKenneth E. Jansen * This function takes a long long pointer and assign (end) phiotmrc value to it 31459599516SKenneth E. Jansen */ 31559599516SKenneth E. Jansen void endTimer(double* end) { 31659599516SKenneth E. Jansen if( !PRINT_PERF ) return; 31759599516SKenneth E. Jansen *end = phiotmrc(); 31859599516SKenneth E. Jansen MPI_Barrier(MPI_COMM_WORLD); 31959599516SKenneth E. Jansen } 32059599516SKenneth E. Jansen 32159599516SKenneth E. Jansen /** 32259599516SKenneth E. Jansen * choose to print some performance results (or not) according to 32359599516SKenneth E. Jansen * the PRINT_PERF macro 32459599516SKenneth E. Jansen */ 32559599516SKenneth E. Jansen void printPerf( 32659599516SKenneth E. Jansen const char* func_name, 32759599516SKenneth E. Jansen double start, 32859599516SKenneth E. Jansen double end, 3292dd307a1SCameron Smith unsigned long datasize, 33059599516SKenneth E. Jansen int printdatainfo, 33159599516SKenneth E. Jansen const char* extra_msg) { 33259599516SKenneth E. Jansen if( !PRINT_PERF ) return; 3332dd307a1SCameron Smith unsigned long data_size = datasize; 33459599516SKenneth E. Jansen double time = end - start; 3352dd307a1SCameron Smith unsigned long isizemin,isizemax,isizetot; 33659599516SKenneth E. Jansen double sizemin,sizemax,sizeavg,sizetot,rate; 33759599516SKenneth E. Jansen double tmin, tmax, tavg, ttot; 33859599516SKenneth E. Jansen 33959599516SKenneth E. Jansen MPI_Allreduce(&time, &tmin,1, MPI_DOUBLE, MPI_MIN, MPI_COMM_WORLD); 34059599516SKenneth E. Jansen MPI_Allreduce(&time, &tmax,1, MPI_DOUBLE, MPI_MAX, MPI_COMM_WORLD); 34159599516SKenneth E. Jansen MPI_Allreduce(&time, &ttot,1, MPI_DOUBLE, MPI_SUM, MPI_COMM_WORLD); 34259599516SKenneth E. Jansen tavg = ttot/mysize; 34359599516SKenneth E. Jansen 34459599516SKenneth E. Jansen if(irank == 0) { 34559599516SKenneth E. Jansen if ( PhastaIONextActiveIndex == 0 ) printf("** 1PFPP "); 34659599516SKenneth E. Jansen else printf("** syncIO "); 34759599516SKenneth E. Jansen printf("%s(): Tmax = %f sec, Tmin = %f sec, Tavg = %f sec", func_name, tmax, tmin, tavg); 34859599516SKenneth E. Jansen } 34959599516SKenneth E. Jansen 35059599516SKenneth E. Jansen if(printdatainfo == 1) { // if printdatainfo ==1, compute I/O rate and block size 35159599516SKenneth E. Jansen MPI_Allreduce(&data_size,&isizemin,1,MPI_LONG_LONG_INT,MPI_MIN,MPI_COMM_WORLD); 35259599516SKenneth E. Jansen MPI_Allreduce(&data_size,&isizemax,1,MPI_LONG_LONG_INT,MPI_MAX,MPI_COMM_WORLD); 35359599516SKenneth E. Jansen MPI_Allreduce(&data_size,&isizetot,1,MPI_LONG_LONG_INT,MPI_SUM,MPI_COMM_WORLD); 35459599516SKenneth E. Jansen 35559599516SKenneth E. Jansen sizemin=(double)(isizemin*inv1024sq); 35659599516SKenneth E. Jansen sizemax=(double)(isizemax*inv1024sq); 35759599516SKenneth E. Jansen sizetot=(double)(isizetot*inv1024sq); 35859599516SKenneth E. Jansen sizeavg=(double)(1.0*sizetot/mysize); 35959599516SKenneth E. Jansen rate=(double)(1.0*sizetot/tmax); 36059599516SKenneth E. Jansen 36159599516SKenneth E. Jansen if( irank == 0) { 362103be424SCameron Smith printf(", Rate = %f MB/s [%s] \n \t\t\t" 363103be424SCameron Smith " block size: Min= %f MB; Max= %f MB; Avg= %f MB; Tot= %f MB\n", 364103be424SCameron Smith rate, extra_msg, sizemin,sizemax,sizeavg,sizetot); 36559599516SKenneth E. Jansen } 36659599516SKenneth E. Jansen } 36759599516SKenneth E. Jansen else { 36859599516SKenneth E. Jansen if(irank == 0) { 36959599516SKenneth E. Jansen printf(" \n"); 37059599516SKenneth E. Jansen //printf(" (%s) \n", extra_msg); 37159599516SKenneth E. Jansen } 37259599516SKenneth E. Jansen } 37359599516SKenneth E. Jansen } 37459599516SKenneth E. Jansen 37559599516SKenneth E. Jansen /** 37659599516SKenneth E. Jansen * This function is normally called at the beginning of a read operation, before 37759599516SKenneth E. Jansen * init function. 37859599516SKenneth E. Jansen * This function (uses rank 0) reads out nfields, nppf, master header size, 37959599516SKenneth E. Jansen * endianess and allocates for masterHeader string. 38059599516SKenneth E. Jansen * These values are essential for following read operations. Rank 0 will bcast 38159599516SKenneth E. Jansen * these values to other ranks in the commm world 38259599516SKenneth E. Jansen * 38359599516SKenneth E. Jansen * If the file set is of old POSIX format, it would throw error and exit 38459599516SKenneth E. Jansen */ 38559599516SKenneth E. Jansen void queryphmpiio(const char filename[],int *nfields, int *nppf) 38659599516SKenneth E. Jansen { 38759599516SKenneth E. Jansen MPI_Comm_rank(MPI_COMM_WORLD, &irank); 38859599516SKenneth E. Jansen MPI_Comm_size(MPI_COMM_WORLD, &mysize); 38959599516SKenneth E. Jansen 39059599516SKenneth E. Jansen if(irank == 0) { 39159599516SKenneth E. Jansen FILE * fileHandle; 39259599516SKenneth E. Jansen char* fname = StringStripper( filename ); 39359599516SKenneth E. Jansen 39459599516SKenneth E. Jansen fileHandle = fopen (fname,"rb"); 39559599516SKenneth E. Jansen if (fileHandle == NULL ) { 39659599516SKenneth E. Jansen printf("\nError: File %s doesn't exist! Please check!\n",fname); 39759599516SKenneth E. Jansen } 39859599516SKenneth E. Jansen else { 39959599516SKenneth E. Jansen SerialFile =(serial_file *)calloc( 1, sizeof( serial_file) ); 40059599516SKenneth E. Jansen int meta_size_limit = VERSION_INFO_HEADER_SIZE; 40159599516SKenneth E. Jansen SerialFile->masterHeader = (char *)malloc( meta_size_limit ); 40259599516SKenneth E. Jansen fread(SerialFile->masterHeader, 1, meta_size_limit, fileHandle); 40359599516SKenneth E. Jansen 40459599516SKenneth E. Jansen char read_out_tag[MAX_FIELDS_NAME_LENGTH]; 40559599516SKenneth E. Jansen char version[MAX_FIELDS_NAME_LENGTH/4]; 40659599516SKenneth E. Jansen int mhsize; 40759599516SKenneth E. Jansen char * token; 40859599516SKenneth E. Jansen int magic_number; 40959599516SKenneth E. Jansen 41059599516SKenneth E. Jansen memcpy( read_out_tag, 41159599516SKenneth E. Jansen SerialFile->masterHeader, 41259599516SKenneth E. Jansen MAX_FIELDS_NAME_LENGTH-1 ); 41359599516SKenneth E. Jansen 41459599516SKenneth E. Jansen if ( cscompare ("MPI_IO_Tag",read_out_tag) ) { 41559599516SKenneth E. Jansen // Test endianess ... 41659599516SKenneth E. Jansen memcpy (&magic_number, 41759599516SKenneth E. Jansen SerialFile->masterHeader + sizeof("MPI_IO_Tag : ")-1, //-1 sizeof returns the size of the string+1 for "\0" 41859599516SKenneth E. Jansen sizeof(int) ); // masterheader should look like "MPI_IO_Tag : 12180 " with 12180 in binary format 41959599516SKenneth E. Jansen 42059599516SKenneth E. Jansen if ( magic_number != ENDIAN_TEST_NUMBER ) { 42159599516SKenneth E. Jansen printf("Endian is different!\n"); 42259599516SKenneth E. Jansen // Will do swap later 42359599516SKenneth E. Jansen } 42459599516SKenneth E. Jansen 42559599516SKenneth E. Jansen // test version, old version, default masterheader size is 4M 42659599516SKenneth E. Jansen // newer version masterheader size is read from first line 42759599516SKenneth E. Jansen memcpy(version, 42859599516SKenneth E. Jansen SerialFile->masterHeader + MAX_FIELDS_NAME_LENGTH/2, 42959599516SKenneth E. Jansen MAX_FIELDS_NAME_LENGTH/4 - 1); //TODO: why -1? 43059599516SKenneth E. Jansen 43159599516SKenneth E. Jansen if( cscompare ("version",version) ) { 43259599516SKenneth E. Jansen // if there is "version" tag in the file, then it is newer format 43359599516SKenneth E. Jansen // read master header size from here, otherwise use default 43459599516SKenneth E. Jansen // Note: if version is "1", we know mhsize is at 3/4 place... 43559599516SKenneth E. Jansen 43659599516SKenneth E. Jansen token = strtok(version, ":"); 43759599516SKenneth E. Jansen token = strtok(NULL, " ,;<>" ); 43859599516SKenneth E. Jansen int iversion = atoi(token); 43959599516SKenneth E. Jansen 44059599516SKenneth E. Jansen if( iversion == 1) { 44159599516SKenneth E. Jansen memcpy( &mhsize, 44259599516SKenneth E. Jansen SerialFile->masterHeader + MAX_FIELDS_NAME_LENGTH/4*3 + sizeof("mhsize : ")-1, 44359599516SKenneth E. Jansen sizeof(int)); 44459599516SKenneth E. Jansen if ( magic_number != ENDIAN_TEST_NUMBER ) 44559599516SKenneth E. Jansen SwapArrayByteOrder(&mhsize, sizeof(int), 1); 44659599516SKenneth E. Jansen 44759599516SKenneth E. Jansen if( mhsize > DefaultMHSize ) { 44859599516SKenneth E. Jansen //if actual headersize is larger than default, let's re-read 44959599516SKenneth E. Jansen free(SerialFile->masterHeader); 45059599516SKenneth E. Jansen SerialFile->masterHeader = (char *)malloc(mhsize); 45159599516SKenneth E. Jansen fseek(fileHandle, 0, SEEK_SET); // reset the file stream position 45259599516SKenneth E. Jansen fread(SerialFile->masterHeader,1,mhsize,fileHandle); 45359599516SKenneth E. Jansen } 45459599516SKenneth E. Jansen } 45559599516SKenneth E. Jansen //TODO: check if this is a valid int?? 45659599516SKenneth E. Jansen MasterHeaderSize = mhsize; 45759599516SKenneth E. Jansen } 45859599516SKenneth E. Jansen else { // else it's version 0's format w/o version tag, implicating MHSize=4M 45959599516SKenneth E. Jansen MasterHeaderSize = DefaultMHSize; 46059599516SKenneth E. Jansen } 46159599516SKenneth E. Jansen 46259599516SKenneth E. Jansen memcpy( read_out_tag, 46359599516SKenneth E. Jansen SerialFile->masterHeader+MAX_FIELDS_NAME_LENGTH+1, 46459599516SKenneth E. Jansen MAX_FIELDS_NAME_LENGTH ); //TODO: why +1 46559599516SKenneth E. Jansen 46659599516SKenneth E. Jansen // Read in # fields ... 46759599516SKenneth E. Jansen token = strtok( read_out_tag, ":" ); 46859599516SKenneth E. Jansen token = strtok( NULL," ,;<>" ); 46959599516SKenneth E. Jansen *nfields = atoi( token ); 47059599516SKenneth E. Jansen if ( *nfields > MAX_FIELDS_NUMBER) { 47159599516SKenneth E. Jansen printf("Error queryphmpiio: nfields is larger than MAX_FIELDS_NUMBER!\n"); 47259599516SKenneth E. Jansen } 47359599516SKenneth E. Jansen SerialFile->nfields=*nfields; //TODO: sanity check of this int? 47459599516SKenneth E. Jansen 47559599516SKenneth E. Jansen memcpy( read_out_tag, 47659599516SKenneth E. Jansen SerialFile->masterHeader + MAX_FIELDS_NAME_LENGTH * 2 47759599516SKenneth E. Jansen + *nfields * MAX_FIELDS_NAME_LENGTH, 47859599516SKenneth E. Jansen MAX_FIELDS_NAME_LENGTH); 47959599516SKenneth E. Jansen 48059599516SKenneth E. Jansen token = strtok( read_out_tag, ":" ); 48159599516SKenneth E. Jansen token = strtok( NULL," ,;<>" ); 48259599516SKenneth E. Jansen *nppf = atoi( token ); 48359599516SKenneth E. Jansen SerialFile->nppf=*nppf; //TODO: sanity check of int 48459599516SKenneth E. Jansen } // end of if("MPI_IO_TAG") 48559599516SKenneth E. Jansen else { 48659599516SKenneth E. Jansen printf("Error queryphmpiio: The file you opened is not of syncIO new format, please check! read_out_tag = %s\n",read_out_tag); 48759599516SKenneth E. Jansen exit(1); 48859599516SKenneth E. Jansen } 48959599516SKenneth E. Jansen fclose(fileHandle); 49059599516SKenneth E. Jansen free(SerialFile->masterHeader); 49159599516SKenneth E. Jansen free(SerialFile); 49259599516SKenneth E. Jansen } //end of else 49359599516SKenneth E. Jansen free(fname); 49459599516SKenneth E. Jansen } 49559599516SKenneth E. Jansen 49659599516SKenneth E. Jansen // Bcast value to every one 49759599516SKenneth E. Jansen MPI_Bcast( nfields, 1, MPI_INT, 0, MPI_COMM_WORLD ); 49859599516SKenneth E. Jansen MPI_Bcast( nppf, 1, MPI_INT, 0, MPI_COMM_WORLD ); 49959599516SKenneth E. Jansen MPI_Bcast( &MasterHeaderSize, 1, MPI_INT, 0, MPI_COMM_WORLD ); 500*a746c838SCameron Smith phprintf("Info queryphmpiio: myrank = %d, MasterHeaderSize = %d\n", irank, MasterHeaderSize); 50159599516SKenneth E. Jansen } 50259599516SKenneth E. Jansen 50359599516SKenneth E. Jansen /** 50459599516SKenneth E. Jansen * This function computes the right master header size (round to size of 2^n). 50559599516SKenneth E. Jansen * This is only needed for file format version 1 in "write" mode. 50659599516SKenneth E. Jansen */ 50759599516SKenneth E. Jansen int computeMHSize(int nfields, int nppf, int version) { 50810d56689SCameron Smith int mhsize=0; 50959599516SKenneth E. Jansen if(version == 1) { 51059599516SKenneth E. Jansen //int meta_info_size = (2+nfields+1) * MAX_FIELDS_NAME_LENGTH; // 2 is MPI_IO_TAG and nFields, the others 1 is nppf 51159599516SKenneth E. Jansen int meta_info_size = VERSION_INFO_HEADER_SIZE; 5122dd307a1SCameron Smith int actual_size = nfields * nppf * sizeof(unsigned long) + meta_info_size; 51359599516SKenneth E. Jansen //printf("actual_size = %d, offset table size = %d\n", actual_size, nfields * nppf * sizeof(long long)); 51459599516SKenneth E. Jansen if (actual_size > DefaultMHSize) { 51559599516SKenneth E. Jansen mhsize = (int) ceil( (double) actual_size/DefaultMHSize); // it's rounded to ceiling of this value 51659599516SKenneth E. Jansen mhsize *= DefaultMHSize; 51759599516SKenneth E. Jansen } 51859599516SKenneth E. Jansen else { 51959599516SKenneth E. Jansen mhsize = DefaultMHSize; 52059599516SKenneth E. Jansen } 521b744cbcaSCameron Smith } else { 522b744cbcaSCameron Smith int rank = 0; 523b744cbcaSCameron Smith MPI_Comm_rank(MPI_COMM_WORLD, &rank); 524b744cbcaSCameron Smith if(!rank) { 525b744cbcaSCameron Smith fprintf(stderr, 526b744cbcaSCameron Smith "ERROR invalid version passed to %s... exiting\n", __func__); 527b744cbcaSCameron Smith exit(EXIT_FAILURE); 528b744cbcaSCameron Smith } 52959599516SKenneth E. Jansen } 53059599516SKenneth E. Jansen return mhsize; 53159599516SKenneth E. Jansen } 53259599516SKenneth E. Jansen 53359599516SKenneth E. Jansen /** 53459599516SKenneth E. Jansen * Computes correct color of a rank according to number of files. 53559599516SKenneth E. Jansen */ 53659599516SKenneth E. Jansen extern "C" int computeColor( int myrank, int numprocs, int nfiles) { 53759599516SKenneth E. Jansen int color = 53859599516SKenneth E. Jansen (int)(myrank / (numprocs / nfiles)); 53959599516SKenneth E. Jansen return color; 54059599516SKenneth E. Jansen } 54159599516SKenneth E. Jansen 54259599516SKenneth E. Jansen 54359599516SKenneth E. Jansen /** 54459599516SKenneth E. Jansen * Check the file descriptor. 54559599516SKenneth E. Jansen */ 546103be424SCameron Smith void checkFileDescriptor(const char fctname[], int* fileDescriptor ) { 54759599516SKenneth E. Jansen if ( *fileDescriptor < 0 ) { 54859599516SKenneth E. Jansen printf("Error: File descriptor = %d in %s\n",*fileDescriptor,fctname); 54959599516SKenneth E. Jansen exit(1); 55059599516SKenneth E. Jansen } 55159599516SKenneth E. Jansen } 55259599516SKenneth E. Jansen 55359599516SKenneth E. Jansen /** 55459599516SKenneth E. Jansen * Initialize the file struct members and allocate space for file struct 55559599516SKenneth E. Jansen * buffers. 55659599516SKenneth E. Jansen * 55759599516SKenneth E. Jansen * Note: this function is only called when we are using new format. Old POSIX 55859599516SKenneth E. Jansen * format should skip this routine and call openfile() directly instead. 55959599516SKenneth E. Jansen */ 56059599516SKenneth E. Jansen int initphmpiio( int *nfields, int *nppf, int *nfiles, int *filehandle, const char mode[]) 56159599516SKenneth E. Jansen { 56259599516SKenneth E. Jansen // we init irank again in case query not called (e.g. syncIO write case) 56359599516SKenneth E. Jansen MPI_Comm_rank(MPI_COMM_WORLD, &irank); 56459599516SKenneth E. Jansen MPI_Comm_size(MPI_COMM_WORLD, &mysize); 56559599516SKenneth E. Jansen 566*a746c838SCameron Smith phprintf("Info initphmpiio: entering function, myrank = %d, MasterHeaderSize = %d, nfields %d, nppf %d, nfiles %d\n", irank, MasterHeaderSize, *nfields, *nppf, *nfiles); 56759599516SKenneth E. Jansen 56859599516SKenneth E. Jansen double timer_start, timer_end; 56959599516SKenneth E. Jansen startTimer(&timer_start); 57059599516SKenneth E. Jansen 57159599516SKenneth E. Jansen char* imode = StringStripper( mode ); 57259599516SKenneth E. Jansen 57359599516SKenneth E. Jansen // Note: if it's read, we presume query was called prior to init and 57459599516SKenneth E. Jansen // MasterHeaderSize is already set to correct value from parsing header 57559599516SKenneth E. Jansen // otherwise it's write then it needs some computation to be set 57659599516SKenneth E. Jansen if ( cscompare( "read", imode ) ) { 57759599516SKenneth E. Jansen // do nothing 57859599516SKenneth E. Jansen } 57959599516SKenneth E. Jansen else if( cscompare( "write", imode ) ) { 58059599516SKenneth E. Jansen MasterHeaderSize = computeMHSize(*nfields, *nppf, LATEST_WRITE_VERSION); 58159599516SKenneth E. Jansen } 58259599516SKenneth E. Jansen else { 58359599516SKenneth E. Jansen printf("Error initphmpiio: can't recognize the mode %s", imode); 58459599516SKenneth E. Jansen exit(1); 58559599516SKenneth E. Jansen } 58659599516SKenneth E. Jansen free ( imode ); 58759599516SKenneth E. Jansen 588*a746c838SCameron Smith phprintf("Info initphmpiio: myrank = %d, MasterHeaderSize = %d\n", irank, MasterHeaderSize); 58959599516SKenneth E. Jansen 59059599516SKenneth E. Jansen int i, j; 59159599516SKenneth E. Jansen 59259599516SKenneth E. Jansen if( PhastaIONextActiveIndex == MAX_PHASTA_FILES ) { 59359599516SKenneth E. Jansen printf("Error initphmpiio: PhastaIONextActiveIndex = MAX_PHASTA_FILES"); 59459599516SKenneth E. Jansen endTimer(&timer_end); 59559599516SKenneth E. Jansen printPerf("initphmpiio", timer_start, timer_end, 0, 0, ""); 59659599516SKenneth E. Jansen return MAX_PHASTA_FILES_EXCEEDED; 59759599516SKenneth E. Jansen } 59859599516SKenneth E. Jansen // else if( PhastaIONextActiveIndex == 0 ) //Hang in debug mode on Intrepid 59959599516SKenneth E. Jansen // { 60059599516SKenneth E. Jansen // for( i = 0; i < MAX_PHASTA_FILES; i++ ); 60159599516SKenneth E. Jansen // { 60259599516SKenneth E. Jansen // PhastaIOActiveFiles[i] = NULL; 60359599516SKenneth E. Jansen // } 60459599516SKenneth E. Jansen // } 60559599516SKenneth E. Jansen 60659599516SKenneth E. Jansen 60759599516SKenneth E. Jansen PhastaIOActiveFiles[PhastaIONextActiveIndex] = (phastaio_file_t *)calloc( 1, sizeof( phastaio_file_t) ); 60859599516SKenneth E. Jansen 60959599516SKenneth E. Jansen i = PhastaIONextActiveIndex; 61059599516SKenneth E. Jansen PhastaIONextActiveIndex++; 61159599516SKenneth E. Jansen 61259599516SKenneth E. Jansen //PhastaIOActiveFiles[i]->next_start_address = 2*TWO_MEGABYTE; 61359599516SKenneth E. Jansen 61459599516SKenneth E. Jansen PhastaIOActiveFiles[i]->next_start_address = MasterHeaderSize; // what does this mean??? TODO 61559599516SKenneth E. Jansen 61659599516SKenneth E. Jansen PhastaIOActiveFiles[i]->Wrong_Endian = false; 61759599516SKenneth E. Jansen 61859599516SKenneth E. Jansen PhastaIOActiveFiles[i]->nFields = *nfields; 61959599516SKenneth E. Jansen PhastaIOActiveFiles[i]->nPPF = *nppf; 62059599516SKenneth E. Jansen PhastaIOActiveFiles[i]->nFiles = *nfiles; 62159599516SKenneth E. Jansen MPI_Comm_rank(MPI_COMM_WORLD, &(PhastaIOActiveFiles[i]->myrank)); 62259599516SKenneth E. Jansen MPI_Comm_size(MPI_COMM_WORLD, &(PhastaIOActiveFiles[i]->numprocs)); 62359599516SKenneth E. Jansen 62459599516SKenneth E. Jansen 62559599516SKenneth E. Jansen if( *nfiles > 1 ) { // split the ranks according to each mpiio file 62659599516SKenneth E. Jansen 62759599516SKenneth E. Jansen if ( s_assign_local_comm == 0) { // call mpi_comm_split for the first (and only) time 62859599516SKenneth E. Jansen 62959599516SKenneth E. Jansen if (PhastaIOActiveFiles[i]->myrank == 0) printf("Building subcommunicator\n"); 63059599516SKenneth E. Jansen 63159599516SKenneth E. Jansen int color = computeColor(PhastaIOActiveFiles[i]->myrank, PhastaIOActiveFiles[i]->numprocs, PhastaIOActiveFiles[i]->nFiles); 63259599516SKenneth E. Jansen MPI_Comm_split(MPI_COMM_WORLD, 63359599516SKenneth E. Jansen color, 63459599516SKenneth E. Jansen PhastaIOActiveFiles[i]->myrank, 63559599516SKenneth E. Jansen &(PhastaIOActiveFiles[i]->local_comm)); 63659599516SKenneth E. Jansen MPI_Comm_size(PhastaIOActiveFiles[i]->local_comm, 63759599516SKenneth E. Jansen &(PhastaIOActiveFiles[i]->local_numprocs)); 63859599516SKenneth E. Jansen MPI_Comm_rank(PhastaIOActiveFiles[i]->local_comm, 63959599516SKenneth E. Jansen &(PhastaIOActiveFiles[i]->local_myrank)); 64059599516SKenneth E. Jansen 64159599516SKenneth E. Jansen // back up now these variables so that we do not need to call comm_split again 64259599516SKenneth E. Jansen s_local_comm = PhastaIOActiveFiles[i]->local_comm; 64359599516SKenneth E. Jansen s_local_size = PhastaIOActiveFiles[i]->local_numprocs; 64459599516SKenneth E. Jansen s_local_rank = PhastaIOActiveFiles[i]->local_myrank; 64559599516SKenneth E. Jansen s_assign_local_comm = 1; 64659599516SKenneth E. Jansen } 64759599516SKenneth E. Jansen else { // recycle the subcommunicator 64859599516SKenneth E. Jansen if (PhastaIOActiveFiles[i]->myrank == 0) printf("Recycling subcommunicator\n"); 64959599516SKenneth E. Jansen PhastaIOActiveFiles[i]->local_comm = s_local_comm; 65059599516SKenneth E. Jansen PhastaIOActiveFiles[i]->local_numprocs = s_local_size; 65159599516SKenneth E. Jansen PhastaIOActiveFiles[i]->local_myrank = s_local_rank; 65259599516SKenneth E. Jansen } 65359599516SKenneth E. Jansen } 65459599516SKenneth E. Jansen else { // *nfiles == 1 here - no need to call mpi_comm_split here 65559599516SKenneth E. Jansen 65659599516SKenneth E. Jansen if (PhastaIOActiveFiles[i]->myrank == 0) printf("Bypassing subcommunicator\n"); 65759599516SKenneth E. Jansen PhastaIOActiveFiles[i]->local_comm = MPI_COMM_WORLD; 65859599516SKenneth E. Jansen PhastaIOActiveFiles[i]->local_numprocs = PhastaIOActiveFiles[i]->numprocs; 65959599516SKenneth E. Jansen PhastaIOActiveFiles[i]->local_myrank = PhastaIOActiveFiles[i]->myrank; 66059599516SKenneth E. Jansen 66159599516SKenneth E. Jansen } 66259599516SKenneth E. Jansen 66359599516SKenneth E. Jansen PhastaIOActiveFiles[i]->nppp = 66459599516SKenneth E. Jansen PhastaIOActiveFiles[i]->nPPF/PhastaIOActiveFiles[i]->local_numprocs; 66559599516SKenneth E. Jansen 66659599516SKenneth E. Jansen PhastaIOActiveFiles[i]->start_id = PhastaIOActiveFiles[i]->nPPF * 66759599516SKenneth E. Jansen (int)(PhastaIOActiveFiles[i]->myrank/PhastaIOActiveFiles[i]->local_numprocs) + 66859599516SKenneth E. Jansen (PhastaIOActiveFiles[i]->local_myrank * PhastaIOActiveFiles[i]->nppp); 66959599516SKenneth E. Jansen 67059599516SKenneth E. Jansen PhastaIOActiveFiles[i]->my_offset_table = 6712dd307a1SCameron Smith ( unsigned long ** ) calloc( MAX_FIELDS_NUMBER , sizeof( unsigned long *) ); 67259599516SKenneth E. Jansen 67359599516SKenneth E. Jansen PhastaIOActiveFiles[i]->my_read_table = 6742dd307a1SCameron Smith ( unsigned long ** ) calloc( MAX_FIELDS_NUMBER , sizeof( unsigned long *) ); 67559599516SKenneth E. Jansen 67659599516SKenneth E. Jansen for (j=0; j<*nfields; j++) 67759599516SKenneth E. Jansen { 67859599516SKenneth E. Jansen PhastaIOActiveFiles[i]->my_offset_table[j] = 6792dd307a1SCameron Smith ( unsigned long * ) calloc( PhastaIOActiveFiles[i]->nppp , sizeof( unsigned long) ); 68059599516SKenneth E. Jansen 68159599516SKenneth E. Jansen PhastaIOActiveFiles[i]->my_read_table[j] = 6822dd307a1SCameron Smith ( unsigned long * ) calloc( PhastaIOActiveFiles[i]->nppp , sizeof( unsigned long) ); 68359599516SKenneth E. Jansen } 68459599516SKenneth E. Jansen *filehandle = i; 68559599516SKenneth E. Jansen 68659599516SKenneth E. Jansen PhastaIOActiveFiles[i]->master_header = (char *)calloc(MasterHeaderSize,sizeof( char )); 68759599516SKenneth E. Jansen PhastaIOActiveFiles[i]->double_chunk = (double *)calloc(1,sizeof( double )); 68859599516SKenneth E. Jansen PhastaIOActiveFiles[i]->int_chunk = (int *)calloc(1,sizeof( int )); 68959599516SKenneth E. Jansen PhastaIOActiveFiles[i]->read_double_chunk = (double *)calloc(1,sizeof( double )); 69059599516SKenneth E. Jansen PhastaIOActiveFiles[i]->read_int_chunk = (int *)calloc(1,sizeof( int )); 69159599516SKenneth E. Jansen 69259599516SKenneth E. Jansen // Time monitoring 69359599516SKenneth E. Jansen endTimer(&timer_end); 69459599516SKenneth E. Jansen printPerf("initphmpiio", timer_start, timer_end, 0, 0, ""); 69559599516SKenneth E. Jansen 69659599516SKenneth E. Jansen phprintf_0("Info initphmpiio: quiting function"); 69759599516SKenneth E. Jansen 69859599516SKenneth E. Jansen return i; 69959599516SKenneth E. Jansen } 70059599516SKenneth E. Jansen 70159599516SKenneth E. Jansen /** 70259599516SKenneth E. Jansen * Destruct the file struct and free buffers allocated in init function. 70359599516SKenneth E. Jansen */ 70459599516SKenneth E. Jansen void finalizephmpiio( int *fileDescriptor ) 70559599516SKenneth E. Jansen { 70659599516SKenneth E. Jansen double timer_start, timer_end; 70759599516SKenneth E. Jansen startTimer(&timer_start); 70859599516SKenneth E. Jansen 70959599516SKenneth E. Jansen int i, j; 71059599516SKenneth E. Jansen i = *fileDescriptor; 71159599516SKenneth E. Jansen //PhastaIONextActiveIndex--; 71259599516SKenneth E. Jansen 71359599516SKenneth E. Jansen /* //free the offset table for this phasta file */ 71459599516SKenneth E. Jansen //for(j=0; j<MAX_FIELDS_NUMBER; j++) //Danger: undefined behavior for my_*_table.[j] not allocated or not initialized to NULL 71559599516SKenneth E. Jansen for(j=0; j<PhastaIOActiveFiles[i]->nFields; j++) 71659599516SKenneth E. Jansen { 71759599516SKenneth E. Jansen free( PhastaIOActiveFiles[i]->my_offset_table[j]); 71859599516SKenneth E. Jansen free( PhastaIOActiveFiles[i]->my_read_table[j]); 71959599516SKenneth E. Jansen } 72059599516SKenneth E. Jansen free ( PhastaIOActiveFiles[i]->my_offset_table ); 72159599516SKenneth E. Jansen free ( PhastaIOActiveFiles[i]->my_read_table ); 72259599516SKenneth E. Jansen free ( PhastaIOActiveFiles[i]->master_header ); 72359599516SKenneth E. Jansen free ( PhastaIOActiveFiles[i]->double_chunk ); 72459599516SKenneth E. Jansen free ( PhastaIOActiveFiles[i]->int_chunk ); 72559599516SKenneth E. Jansen free ( PhastaIOActiveFiles[i]->read_double_chunk ); 72659599516SKenneth E. Jansen free ( PhastaIOActiveFiles[i]->read_int_chunk ); 72759599516SKenneth E. Jansen 728946a6cddSCameron Smith if( PhastaIOActiveFiles[i]->nFiles > 1 && s_assign_local_comm ) { // the comm was split 729946a6cddSCameron Smith if (PhastaIOActiveFiles[i]->myrank == 0) printf("Freeing subcommunicator\n"); 730946a6cddSCameron Smith s_assign_local_comm = 0; 731946a6cddSCameron Smith MPI_Comm_free(&(PhastaIOActiveFiles[i]->local_comm)); 732946a6cddSCameron Smith } 733946a6cddSCameron Smith 73459599516SKenneth E. Jansen free( PhastaIOActiveFiles[i]); 73559599516SKenneth E. Jansen 73659599516SKenneth E. Jansen endTimer(&timer_end); 73759599516SKenneth E. Jansen printPerf("finalizempiio", timer_start, timer_end, 0, 0, ""); 73859599516SKenneth E. Jansen 73959599516SKenneth E. Jansen PhastaIONextActiveIndex--; 74059599516SKenneth E. Jansen } 74159599516SKenneth E. Jansen 74259599516SKenneth E. Jansen 74359599516SKenneth E. Jansen /** 74459599516SKenneth E. Jansen * Special init for M2N in order to create a subcommunicator for the reduced solution (requires PRINT_PERF to be false for now) 74559599516SKenneth E. Jansen * Initialize the file struct members and allocate space for file struct buffers. 74659599516SKenneth E. Jansen * 74759599516SKenneth E. Jansen * Note: this function is only called when we are using new format. Old POSIX 74859599516SKenneth E. Jansen * format should skip this routine and call openfile() directly instead. 74959599516SKenneth E. Jansen */ 75059599516SKenneth E. Jansen int initphmpiiosub( int *nfields, int *nppf, int *nfiles, int *filehandle, const char mode[],MPI_Comm my_local_comm) 75159599516SKenneth E. Jansen { 75259599516SKenneth E. Jansen // we init irank again in case query not called (e.g. syncIO write case) 75359599516SKenneth E. Jansen 75459599516SKenneth E. Jansen MPI_Comm_rank(my_local_comm, &irank); 75559599516SKenneth E. Jansen MPI_Comm_size(my_local_comm, &mysize); 75659599516SKenneth E. Jansen 757*a746c838SCameron Smith phprintf("Info initphmpiio: entering function, myrank = %d, MasterHeaderSize = %d\n", irank, MasterHeaderSize); 75859599516SKenneth E. Jansen 75959599516SKenneth E. Jansen double timer_start, timer_end; 76059599516SKenneth E. Jansen startTimer(&timer_start); 76159599516SKenneth E. Jansen 76259599516SKenneth E. Jansen char* imode = StringStripper( mode ); 76359599516SKenneth E. Jansen 76459599516SKenneth E. Jansen // Note: if it's read, we presume query was called prior to init and 76559599516SKenneth E. Jansen // MasterHeaderSize is already set to correct value from parsing header 76659599516SKenneth E. Jansen // otherwise it's write then it needs some computation to be set 76759599516SKenneth E. Jansen if ( cscompare( "read", imode ) ) { 76859599516SKenneth E. Jansen // do nothing 76959599516SKenneth E. Jansen } 77059599516SKenneth E. Jansen else if( cscompare( "write", imode ) ) { 77159599516SKenneth E. Jansen MasterHeaderSize = computeMHSize(*nfields, *nppf, LATEST_WRITE_VERSION); 77259599516SKenneth E. Jansen } 77359599516SKenneth E. Jansen else { 77459599516SKenneth E. Jansen printf("Error initphmpiio: can't recognize the mode %s", imode); 77559599516SKenneth E. Jansen exit(1); 77659599516SKenneth E. Jansen } 77759599516SKenneth E. Jansen free ( imode ); 77859599516SKenneth E. Jansen 779*a746c838SCameron Smith phprintf("Info initphmpiio: myrank = %d, MasterHeaderSize = %d\n", irank, MasterHeaderSize); 78059599516SKenneth E. Jansen 78159599516SKenneth E. Jansen int i, j; 78259599516SKenneth E. Jansen 78359599516SKenneth E. Jansen if( PhastaIONextActiveIndex == MAX_PHASTA_FILES ) { 78459599516SKenneth E. Jansen printf("Error initphmpiio: PhastaIONextActiveIndex = MAX_PHASTA_FILES"); 78559599516SKenneth E. Jansen endTimer(&timer_end); 78659599516SKenneth E. Jansen printPerf("initphmpiio", timer_start, timer_end, 0, 0, ""); 78759599516SKenneth E. Jansen return MAX_PHASTA_FILES_EXCEEDED; 78859599516SKenneth E. Jansen } 78959599516SKenneth E. Jansen // else if( PhastaIONextActiveIndex == 0 ) //Hang in debug mode on Intrepid 79059599516SKenneth E. Jansen // { 79159599516SKenneth E. Jansen // for( i = 0; i < MAX_PHASTA_FILES; i++ ); 79259599516SKenneth E. Jansen // { 79359599516SKenneth E. Jansen // PhastaIOActiveFiles[i] = NULL; 79459599516SKenneth E. Jansen // } 79559599516SKenneth E. Jansen // } 79659599516SKenneth E. Jansen 79759599516SKenneth E. Jansen 79859599516SKenneth E. Jansen PhastaIOActiveFiles[PhastaIONextActiveIndex] = (phastaio_file_t *)calloc( 1, sizeof( phastaio_file_t) ); 79959599516SKenneth E. Jansen 80059599516SKenneth E. Jansen i = PhastaIONextActiveIndex; 80159599516SKenneth E. Jansen PhastaIONextActiveIndex++; 80259599516SKenneth E. Jansen 80359599516SKenneth E. Jansen //PhastaIOActiveFiles[i]->next_start_address = 2*TWO_MEGABYTE; 80459599516SKenneth E. Jansen 80559599516SKenneth E. Jansen PhastaIOActiveFiles[i]->next_start_address = MasterHeaderSize; // what does this mean??? TODO 80659599516SKenneth E. Jansen 80759599516SKenneth E. Jansen PhastaIOActiveFiles[i]->Wrong_Endian = false; 80859599516SKenneth E. Jansen 80959599516SKenneth E. Jansen PhastaIOActiveFiles[i]->nFields = *nfields; 81059599516SKenneth E. Jansen PhastaIOActiveFiles[i]->nPPF = *nppf; 81159599516SKenneth E. Jansen PhastaIOActiveFiles[i]->nFiles = *nfiles; 81259599516SKenneth E. Jansen MPI_Comm_rank(my_local_comm, &(PhastaIOActiveFiles[i]->myrank)); 81359599516SKenneth E. Jansen MPI_Comm_size(my_local_comm, &(PhastaIOActiveFiles[i]->numprocs)); 81459599516SKenneth E. Jansen 81559599516SKenneth E. Jansen int color = computeColor(PhastaIOActiveFiles[i]->myrank, PhastaIOActiveFiles[i]->numprocs, PhastaIOActiveFiles[i]->nFiles); 81659599516SKenneth E. Jansen MPI_Comm_split(my_local_comm, 81759599516SKenneth E. Jansen color, 81859599516SKenneth E. Jansen PhastaIOActiveFiles[i]->myrank, 81959599516SKenneth E. Jansen &(PhastaIOActiveFiles[i]->local_comm)); 82059599516SKenneth E. Jansen MPI_Comm_size(PhastaIOActiveFiles[i]->local_comm, 82159599516SKenneth E. Jansen &(PhastaIOActiveFiles[i]->local_numprocs)); 82259599516SKenneth E. Jansen MPI_Comm_rank(PhastaIOActiveFiles[i]->local_comm, 82359599516SKenneth E. Jansen &(PhastaIOActiveFiles[i]->local_myrank)); 82459599516SKenneth E. Jansen PhastaIOActiveFiles[i]->nppp = 82559599516SKenneth E. Jansen PhastaIOActiveFiles[i]->nPPF/PhastaIOActiveFiles[i]->local_numprocs; 82659599516SKenneth E. Jansen 82759599516SKenneth E. Jansen PhastaIOActiveFiles[i]->start_id = PhastaIOActiveFiles[i]->nPPF * 82859599516SKenneth E. Jansen (int)(PhastaIOActiveFiles[i]->myrank/PhastaIOActiveFiles[i]->local_numprocs) + 82959599516SKenneth E. Jansen (PhastaIOActiveFiles[i]->local_myrank * PhastaIOActiveFiles[i]->nppp); 83059599516SKenneth E. Jansen 83159599516SKenneth E. Jansen PhastaIOActiveFiles[i]->my_offset_table = 8322dd307a1SCameron Smith ( unsigned long ** ) calloc( MAX_FIELDS_NUMBER , sizeof( unsigned long *) ); 83359599516SKenneth E. Jansen 83459599516SKenneth E. Jansen PhastaIOActiveFiles[i]->my_read_table = 8352dd307a1SCameron Smith ( unsigned long ** ) calloc( MAX_FIELDS_NUMBER , sizeof( unsigned long *) ); 83659599516SKenneth E. Jansen 83759599516SKenneth E. Jansen for (j=0; j<*nfields; j++) 83859599516SKenneth E. Jansen { 83959599516SKenneth E. Jansen PhastaIOActiveFiles[i]->my_offset_table[j] = 8402dd307a1SCameron Smith ( unsigned long * ) calloc( PhastaIOActiveFiles[i]->nppp , sizeof( unsigned long) ); 84159599516SKenneth E. Jansen 84259599516SKenneth E. Jansen PhastaIOActiveFiles[i]->my_read_table[j] = 8432dd307a1SCameron Smith ( unsigned long * ) calloc( PhastaIOActiveFiles[i]->nppp , sizeof( unsigned long) ); 84459599516SKenneth E. Jansen } 84559599516SKenneth E. Jansen *filehandle = i; 84659599516SKenneth E. Jansen 84759599516SKenneth E. Jansen PhastaIOActiveFiles[i]->master_header = (char *)calloc(MasterHeaderSize,sizeof( char )); 84859599516SKenneth E. Jansen PhastaIOActiveFiles[i]->double_chunk = (double *)calloc(1,sizeof( double )); 84959599516SKenneth E. Jansen PhastaIOActiveFiles[i]->int_chunk = (int *)calloc(1,sizeof( int )); 85059599516SKenneth E. Jansen PhastaIOActiveFiles[i]->read_double_chunk = (double *)calloc(1,sizeof( double )); 85159599516SKenneth E. Jansen PhastaIOActiveFiles[i]->read_int_chunk = (int *)calloc(1,sizeof( int )); 85259599516SKenneth E. Jansen 85359599516SKenneth E. Jansen // Time monitoring 85459599516SKenneth E. Jansen endTimer(&timer_end); 85559599516SKenneth E. Jansen printPerf("initphmpiiosub", timer_start, timer_end, 0, 0, ""); 85659599516SKenneth E. Jansen 85759599516SKenneth E. Jansen phprintf_0("Info initphmpiiosub: quiting function"); 85859599516SKenneth E. Jansen 85959599516SKenneth E. Jansen return i; 86059599516SKenneth E. Jansen } 86159599516SKenneth E. Jansen 86259599516SKenneth E. Jansen 86359599516SKenneth E. Jansen 86459599516SKenneth E. Jansen /** open file for both POSIX and MPI-IO syncIO format. 86559599516SKenneth E. Jansen * 86659599516SKenneth E. Jansen * If it's old POSIX format, simply call posix fopen(). 86759599516SKenneth E. Jansen * 86859599516SKenneth E. Jansen * If it's MPI-IO foramt: 86959599516SKenneth E. Jansen * in "read" mode, it builds the header table that points to the offset of 87059599516SKenneth E. Jansen * fields for parts; 87159599516SKenneth E. Jansen * in "write" mode, it opens the file with MPI-IO open routine. 87259599516SKenneth E. Jansen */ 873103be424SCameron Smith void openfile(const char filename[], const char mode[], int* fileDescriptor ) 87459599516SKenneth E. Jansen { 87559599516SKenneth E. Jansen phprintf_0("Info: entering openfile"); 87659599516SKenneth E. Jansen 87759599516SKenneth E. Jansen double timer_start, timer_end; 87859599516SKenneth E. Jansen startTimer(&timer_start); 87959599516SKenneth E. Jansen 88059599516SKenneth E. Jansen if ( PhastaIONextActiveIndex == 0 ) 88159599516SKenneth E. Jansen { 88259599516SKenneth E. Jansen FILE* file=NULL ; 88359599516SKenneth E. Jansen *fileDescriptor = 0; 88459599516SKenneth E. Jansen char* fname = StringStripper( filename ); 88559599516SKenneth E. Jansen char* imode = StringStripper( mode ); 88659599516SKenneth E. Jansen 88759599516SKenneth E. Jansen if ( cscompare( "read", imode ) ) file = fopen(fname, "rb" ); 88859599516SKenneth E. Jansen else if( cscompare( "write", imode ) ) file = fopen(fname, "wb" ); 88959599516SKenneth E. Jansen else if( cscompare( "append", imode ) ) file = fopen(fname, "ab" ); 89059599516SKenneth E. Jansen 89159599516SKenneth E. Jansen if ( !file ){ 89267701978SCameron Smith fprintf(stderr,"Error openfile: unable to open file %s\n",fname); 89359599516SKenneth E. Jansen } else { 89459599516SKenneth E. Jansen fileArray.push_back( file ); 89559599516SKenneth E. Jansen byte_order.push_back( false ); 89659599516SKenneth E. Jansen header_type.push_back( sizeof(int) ); 89759599516SKenneth E. Jansen *fileDescriptor = fileArray.size(); 89859599516SKenneth E. Jansen } 89959599516SKenneth E. Jansen free (fname); 90059599516SKenneth E. Jansen free (imode); 90159599516SKenneth E. Jansen } 90259599516SKenneth E. Jansen else // else it would be parallel I/O, opposed to posix io 90359599516SKenneth E. Jansen { 90459599516SKenneth E. Jansen char* fname = StringStripper( filename ); 90559599516SKenneth E. Jansen char* imode = StringStripper( mode ); 90659599516SKenneth E. Jansen int rc; 90759599516SKenneth E. Jansen int i = *fileDescriptor; 90859599516SKenneth E. Jansen checkFileDescriptor("openfile",&i); 90959599516SKenneth E. Jansen char* token; 91059599516SKenneth E. Jansen 91159599516SKenneth E. Jansen if ( cscompare( "read", imode ) ) 91259599516SKenneth E. Jansen { 91359599516SKenneth E. Jansen // if (PhastaIOActiveFiles[i]->myrank == 0) 91459599516SKenneth E. Jansen // printf("\n **********\nRead open ... ... regular version\n"); 91559599516SKenneth E. Jansen 91659599516SKenneth E. Jansen rc = MPI_File_open( PhastaIOActiveFiles[i]->local_comm, 91759599516SKenneth E. Jansen fname, 91859599516SKenneth E. Jansen MPI_MODE_RDONLY, 91959599516SKenneth E. Jansen MPI_INFO_NULL, 92059599516SKenneth E. Jansen &(PhastaIOActiveFiles[i]->file_handle) ); 92159599516SKenneth E. Jansen 92259599516SKenneth E. Jansen if(rc) 92359599516SKenneth E. Jansen { 92459599516SKenneth E. Jansen *fileDescriptor = UNABLE_TO_OPEN_FILE; 9254d60bba2SCameron Smith int error_string_length; 9264d60bba2SCameron Smith char error_string[4096]; 9274d60bba2SCameron Smith MPI_Error_string(rc, error_string, &error_string_length); 9284d60bba2SCameron Smith fprintf(stderr, "Error openfile: Unable to open file %s! MPI reports \"%s\"\n",fname,error_string); 92959599516SKenneth E. Jansen endTimer(&timer_end); 93059599516SKenneth E. Jansen printPerf("openfile", timer_start, timer_end, 0, 0, ""); 93159599516SKenneth E. Jansen return; 93259599516SKenneth E. Jansen } 93359599516SKenneth E. Jansen 93459599516SKenneth E. Jansen MPI_Status read_tag_status; 93559599516SKenneth E. Jansen char read_out_tag[MAX_FIELDS_NAME_LENGTH]; 93659599516SKenneth E. Jansen int j; 93759599516SKenneth E. Jansen int magic_number; 93859599516SKenneth E. Jansen 93959599516SKenneth E. Jansen if ( PhastaIOActiveFiles[i]->local_myrank == 0 ) { 94059599516SKenneth E. Jansen MPI_File_read_at( PhastaIOActiveFiles[i]->file_handle, 94159599516SKenneth E. Jansen 0, 94259599516SKenneth E. Jansen PhastaIOActiveFiles[i]->master_header, 94359599516SKenneth E. Jansen MasterHeaderSize, 94459599516SKenneth E. Jansen MPI_CHAR, 94559599516SKenneth E. Jansen &read_tag_status ); 94659599516SKenneth E. Jansen } 94759599516SKenneth E. Jansen 94859599516SKenneth E. Jansen MPI_Bcast( PhastaIOActiveFiles[i]->master_header, 94959599516SKenneth E. Jansen MasterHeaderSize, 95059599516SKenneth E. Jansen MPI_CHAR, 95159599516SKenneth E. Jansen 0, 95259599516SKenneth E. Jansen PhastaIOActiveFiles[i]->local_comm ); 95359599516SKenneth E. Jansen 95459599516SKenneth E. Jansen memcpy( read_out_tag, 95559599516SKenneth E. Jansen PhastaIOActiveFiles[i]->master_header, 95659599516SKenneth E. Jansen MAX_FIELDS_NAME_LENGTH-1 ); 95759599516SKenneth E. Jansen 95859599516SKenneth E. Jansen if ( cscompare ("MPI_IO_Tag",read_out_tag) ) 95959599516SKenneth E. Jansen { 96059599516SKenneth E. Jansen // Test endianess ... 96159599516SKenneth E. Jansen memcpy ( &magic_number, 96259599516SKenneth E. Jansen PhastaIOActiveFiles[i]->master_header+sizeof("MPI_IO_Tag : ")-1, //-1 sizeof returns the size of the string+1 for "\0" 96359599516SKenneth E. Jansen sizeof(int) ); // masterheader should look like "MPI_IO_Tag : 12180 " with 12180 in binary format 96459599516SKenneth E. Jansen 96559599516SKenneth E. Jansen if ( magic_number != ENDIAN_TEST_NUMBER ) 96659599516SKenneth E. Jansen { 96759599516SKenneth E. Jansen PhastaIOActiveFiles[i]->Wrong_Endian = true; 96859599516SKenneth E. Jansen } 96959599516SKenneth E. Jansen 97059599516SKenneth E. Jansen memcpy( read_out_tag, 97159599516SKenneth E. Jansen PhastaIOActiveFiles[i]->master_header+MAX_FIELDS_NAME_LENGTH+1, // TODO: WHY +1??? 97259599516SKenneth E. Jansen MAX_FIELDS_NAME_LENGTH ); 97359599516SKenneth E. Jansen 97459599516SKenneth E. Jansen // Read in # fields ... 97559599516SKenneth E. Jansen token = strtok ( read_out_tag, ":" ); 97659599516SKenneth E. Jansen token = strtok( NULL," ,;<>" ); 97759599516SKenneth E. Jansen PhastaIOActiveFiles[i]->nFields = atoi( token ); 97859599516SKenneth E. Jansen 9792dd307a1SCameron Smith unsigned long **header_table; 9802dd307a1SCameron Smith header_table = ( unsigned long ** )calloc(PhastaIOActiveFiles[i]->nFields, sizeof(unsigned long *)); 98159599516SKenneth E. Jansen 98259599516SKenneth E. Jansen for ( j = 0; j < PhastaIOActiveFiles[i]->nFields; j++ ) 98359599516SKenneth E. Jansen { 9842dd307a1SCameron Smith header_table[j]=( unsigned long * ) calloc( PhastaIOActiveFiles[i]->nPPF , sizeof( unsigned long)); 98559599516SKenneth E. Jansen } 98659599516SKenneth E. Jansen 98759599516SKenneth E. Jansen // Read in the offset table ... 98859599516SKenneth E. Jansen for ( j = 0; j < PhastaIOActiveFiles[i]->nFields; j++ ) 98959599516SKenneth E. Jansen { 99059599516SKenneth E. Jansen if ( PhastaIOActiveFiles[i]->local_myrank == 0 ) { 99159599516SKenneth E. Jansen memcpy( header_table[j], 99259599516SKenneth E. Jansen PhastaIOActiveFiles[i]->master_header + 99359599516SKenneth E. Jansen VERSION_INFO_HEADER_SIZE + 9942dd307a1SCameron Smith j * PhastaIOActiveFiles[i]->nPPF * sizeof(unsigned long), 9952dd307a1SCameron Smith PhastaIOActiveFiles[i]->nPPF * sizeof(unsigned long) ); 99659599516SKenneth E. Jansen } 99759599516SKenneth E. Jansen 99859599516SKenneth E. Jansen MPI_Scatter( header_table[j], 99959599516SKenneth E. Jansen PhastaIOActiveFiles[i]->nppp, 100059599516SKenneth E. Jansen MPI_LONG_LONG_INT, 100159599516SKenneth E. Jansen PhastaIOActiveFiles[i]->my_read_table[j], 100259599516SKenneth E. Jansen PhastaIOActiveFiles[i]->nppp, 100359599516SKenneth E. Jansen MPI_LONG_LONG_INT, 100459599516SKenneth E. Jansen 0, 100559599516SKenneth E. Jansen PhastaIOActiveFiles[i]->local_comm ); 100659599516SKenneth E. Jansen 100759599516SKenneth E. Jansen // Swap byte order if endianess is different ... 100859599516SKenneth E. Jansen if ( PhastaIOActiveFiles[i]->Wrong_Endian ) { 100959599516SKenneth E. Jansen SwapArrayByteOrder( PhastaIOActiveFiles[i]->my_read_table[j], 10104187599aSCameron Smith sizeof(unsigned long), 101159599516SKenneth E. Jansen PhastaIOActiveFiles[i]->nppp ); 101259599516SKenneth E. Jansen } 101359599516SKenneth E. Jansen } 101459599516SKenneth E. Jansen 101559599516SKenneth E. Jansen for ( j = 0; j < PhastaIOActiveFiles[i]->nFields; j++ ) { 101659599516SKenneth E. Jansen free ( header_table[j] ); 101759599516SKenneth E. Jansen } 101859599516SKenneth E. Jansen free (header_table); 101959599516SKenneth E. Jansen 102059599516SKenneth E. Jansen } // end of if MPI_IO_TAG 102159599516SKenneth E. Jansen else //else not valid MPI file 102259599516SKenneth E. Jansen { 102359599516SKenneth E. Jansen *fileDescriptor = NOT_A_MPI_FILE; 102459599516SKenneth E. Jansen printf("Error openfile: The file %s you opened is not in syncIO new format, please check again! File descriptor = %d, MasterHeaderSize = %d, read_out_tag = %s\n",fname,*fileDescriptor,MasterHeaderSize,read_out_tag); 102559599516SKenneth E. Jansen //Printing MasterHeaderSize is useful to test a compiler bug on Intrepid BGP 102659599516SKenneth E. Jansen endTimer(&timer_end); 102759599516SKenneth E. Jansen printPerf("openfile", timer_start, timer_end, 0, 0, ""); 102859599516SKenneth E. Jansen return; 102959599516SKenneth E. Jansen } 103059599516SKenneth E. Jansen } // end of if "read" 103159599516SKenneth E. Jansen else if( cscompare( "write", imode ) ) 103259599516SKenneth E. Jansen { 103359599516SKenneth E. Jansen rc = MPI_File_open( PhastaIOActiveFiles[i]->local_comm, 103459599516SKenneth E. Jansen fname, 103559599516SKenneth E. Jansen MPI_MODE_WRONLY | MPI_MODE_CREATE, 103659599516SKenneth E. Jansen MPI_INFO_NULL, 103759599516SKenneth E. Jansen &(PhastaIOActiveFiles[i]->file_handle) ); 10384d60bba2SCameron Smith if(rc != MPI_SUCCESS) 103959599516SKenneth E. Jansen { 104059599516SKenneth E. Jansen *fileDescriptor = UNABLE_TO_OPEN_FILE; 10414d60bba2SCameron Smith int error_string_length; 10424d60bba2SCameron Smith char error_string[4096]; 10434d60bba2SCameron Smith MPI_Error_string(rc, error_string, &error_string_length); 10444d60bba2SCameron Smith fprintf(stderr, "Error openfile: Unable to open file %s! MPI reports \"%s\"\n",fname,error_string); 104559599516SKenneth E. Jansen return; 104659599516SKenneth E. Jansen } 104759599516SKenneth E. Jansen } // end of if "write" 104859599516SKenneth E. Jansen free (fname); 104959599516SKenneth E. Jansen free (imode); 105059599516SKenneth E. Jansen } // end of if FileIndex != 0 105159599516SKenneth E. Jansen 105259599516SKenneth E. Jansen endTimer(&timer_end); 105359599516SKenneth E. Jansen printPerf("openfile", timer_start, timer_end, 0, 0, ""); 105459599516SKenneth E. Jansen } 105559599516SKenneth E. Jansen 105659599516SKenneth E. Jansen /** close file for both POSIX and MPI-IO syncIO format. 105759599516SKenneth E. Jansen * 105859599516SKenneth E. Jansen * If it's old POSIX format, simply call posix fclose(). 105959599516SKenneth E. Jansen * 106059599516SKenneth E. Jansen * If it's MPI-IO foramt: 106159599516SKenneth E. Jansen * in "read" mode, it simply close file with MPI-IO close routine. 106259599516SKenneth E. Jansen * in "write" mode, rank 0 in each group will re-assemble the master header and 106359599516SKenneth E. Jansen * offset table and write to the beginning of file, then close the file. 106459599516SKenneth E. Jansen */ 1065103be424SCameron Smith void closefile( int* fileDescriptor, const char mode[] ) 106659599516SKenneth E. Jansen { 106759599516SKenneth E. Jansen double timer_start, timer_end; 106859599516SKenneth E. Jansen startTimer(&timer_start); 106959599516SKenneth E. Jansen 107059599516SKenneth E. Jansen int i = *fileDescriptor; 107159599516SKenneth E. Jansen checkFileDescriptor("closefile",&i); 107259599516SKenneth E. Jansen 107359599516SKenneth E. Jansen if ( PhastaIONextActiveIndex == 0 ) { 107459599516SKenneth E. Jansen char* imode = StringStripper( mode ); 107559599516SKenneth E. Jansen 107659599516SKenneth E. Jansen if( cscompare( "write", imode ) 107759599516SKenneth E. Jansen || cscompare( "append", imode ) ) { 107859599516SKenneth E. Jansen fflush( fileArray[ *fileDescriptor - 1 ] ); 107959599516SKenneth E. Jansen } 108059599516SKenneth E. Jansen 108159599516SKenneth E. Jansen fclose( fileArray[ *fileDescriptor - 1 ] ); 108259599516SKenneth E. Jansen free (imode); 108359599516SKenneth E. Jansen } 108459599516SKenneth E. Jansen else { 108559599516SKenneth E. Jansen char* imode = StringStripper( mode ); 108659599516SKenneth E. Jansen 108759599516SKenneth E. Jansen //write master header here: 108859599516SKenneth E. Jansen if ( cscompare( "write", imode ) ) { 108959599516SKenneth E. Jansen // if ( PhastaIOActiveFiles[i]->nPPF * PhastaIOActiveFiles[i]->nFields < 2*ONE_MEGABYTE/8 ) //SHOULD BE CHECKED 109059599516SKenneth E. Jansen // MasterHeaderSize = 4*ONE_MEGABYTE; 109159599516SKenneth E. Jansen // else 109259599516SKenneth E. Jansen // MasterHeaderSize = 4*ONE_MEGABYTE + PhastaIOActiveFiles[i]->nPPF * PhastaIOActiveFiles[i]->nFields * 8 - 2*ONE_MEGABYTE; 109359599516SKenneth E. Jansen 109459599516SKenneth E. Jansen MasterHeaderSize = computeMHSize( PhastaIOActiveFiles[i]->nFields, PhastaIOActiveFiles[i]->nPPF, LATEST_WRITE_VERSION); 109559599516SKenneth E. Jansen phprintf_0("Info closefile: myrank = %d, MasterHeaderSize = %d\n", PhastaIOActiveFiles[i]->myrank, MasterHeaderSize); 109659599516SKenneth E. Jansen 109759599516SKenneth E. Jansen MPI_Status write_header_status; 109859599516SKenneth E. Jansen char mpi_tag[MAX_FIELDS_NAME_LENGTH]; 109959599516SKenneth E. Jansen char version[MAX_FIELDS_NAME_LENGTH/4]; 110059599516SKenneth E. Jansen char mhsize[MAX_FIELDS_NAME_LENGTH/4]; 110159599516SKenneth E. Jansen int magic_number = ENDIAN_TEST_NUMBER; 110259599516SKenneth E. Jansen 110359599516SKenneth E. Jansen if ( PhastaIOActiveFiles[i]->local_myrank == 0 ) 110459599516SKenneth E. Jansen { 110559599516SKenneth E. Jansen bzero((void*)mpi_tag,MAX_FIELDS_NAME_LENGTH); 110659599516SKenneth E. Jansen sprintf(mpi_tag, "MPI_IO_Tag : "); 110759599516SKenneth E. Jansen memcpy(PhastaIOActiveFiles[i]->master_header, 110859599516SKenneth E. Jansen mpi_tag, 110959599516SKenneth E. Jansen MAX_FIELDS_NAME_LENGTH); 111059599516SKenneth E. Jansen 111159599516SKenneth E. Jansen bzero((void*)version,MAX_FIELDS_NAME_LENGTH/4); 111259599516SKenneth E. Jansen // this version is "1", print version in ASCII 111359599516SKenneth E. Jansen sprintf(version, "version : %d",1); 111459599516SKenneth E. Jansen memcpy(PhastaIOActiveFiles[i]->master_header + MAX_FIELDS_NAME_LENGTH/2, 111559599516SKenneth E. Jansen version, 111659599516SKenneth E. Jansen MAX_FIELDS_NAME_LENGTH/4); 111759599516SKenneth E. Jansen 111859599516SKenneth E. Jansen // master header size is computed using the formula above 111959599516SKenneth E. Jansen bzero((void*)mhsize,MAX_FIELDS_NAME_LENGTH/4); 112059599516SKenneth E. Jansen sprintf(mhsize, "mhsize : "); 112159599516SKenneth E. Jansen memcpy(PhastaIOActiveFiles[i]->master_header + MAX_FIELDS_NAME_LENGTH/4*3, 112259599516SKenneth E. Jansen mhsize, 112359599516SKenneth E. Jansen MAX_FIELDS_NAME_LENGTH/4); 112459599516SKenneth E. Jansen 112559599516SKenneth E. Jansen bzero((void*)mpi_tag,MAX_FIELDS_NAME_LENGTH); 112659599516SKenneth E. Jansen sprintf(mpi_tag, 112759599516SKenneth E. Jansen "\nnFields : %d\n", 112859599516SKenneth E. Jansen PhastaIOActiveFiles[i]->nFields); 112959599516SKenneth E. Jansen memcpy(PhastaIOActiveFiles[i]->master_header+MAX_FIELDS_NAME_LENGTH, 113059599516SKenneth E. Jansen mpi_tag, 113159599516SKenneth E. Jansen MAX_FIELDS_NAME_LENGTH); 113259599516SKenneth E. Jansen 113359599516SKenneth E. Jansen bzero((void*)mpi_tag,MAX_FIELDS_NAME_LENGTH); 113459599516SKenneth E. Jansen sprintf(mpi_tag, "\nnPPF : %d\n", PhastaIOActiveFiles[i]->nPPF); 113559599516SKenneth E. Jansen memcpy( PhastaIOActiveFiles[i]->master_header+ 113659599516SKenneth E. Jansen PhastaIOActiveFiles[i]->nFields * 113759599516SKenneth E. Jansen MAX_FIELDS_NAME_LENGTH + 113859599516SKenneth E. Jansen MAX_FIELDS_NAME_LENGTH * 2, 113959599516SKenneth E. Jansen mpi_tag, 114059599516SKenneth E. Jansen MAX_FIELDS_NAME_LENGTH); 114159599516SKenneth E. Jansen 114259599516SKenneth E. Jansen memcpy( PhastaIOActiveFiles[i]->master_header+sizeof("MPI_IO_Tag : ")-1, //-1 sizeof returns the size of the string+1 for "\0" 114359599516SKenneth E. Jansen &magic_number, 114459599516SKenneth E. Jansen sizeof(int)); 114559599516SKenneth E. Jansen 114659599516SKenneth E. Jansen memcpy( PhastaIOActiveFiles[i]->master_header+sizeof("mhsize : ") -1 + MAX_FIELDS_NAME_LENGTH/4*3, 114759599516SKenneth E. Jansen &MasterHeaderSize, 114859599516SKenneth E. Jansen sizeof(int)); 114959599516SKenneth E. Jansen } 115059599516SKenneth E. Jansen 115159599516SKenneth E. Jansen int j = 0; 11522dd307a1SCameron Smith unsigned long **header_table; 11532dd307a1SCameron Smith header_table = ( unsigned long ** )calloc(PhastaIOActiveFiles[i]->nFields, sizeof(unsigned long *)); 115459599516SKenneth E. Jansen 115559599516SKenneth E. Jansen for ( j = 0; j < PhastaIOActiveFiles[i]->nFields; j++ ) { 11562dd307a1SCameron Smith header_table[j]=( unsigned long * ) calloc( PhastaIOActiveFiles[i]->nPPF , sizeof( unsigned long)); 115759599516SKenneth E. Jansen } 115859599516SKenneth E. Jansen 115959599516SKenneth E. Jansen //if( irank == 0 ) printf("gonna mpi_gather, myrank = %d\n", irank); 116059599516SKenneth E. Jansen for ( j = 0; j < PhastaIOActiveFiles[i]->nFields; j++ ) { 116159599516SKenneth E. Jansen MPI_Gather( PhastaIOActiveFiles[i]->my_offset_table[j], 116259599516SKenneth E. Jansen PhastaIOActiveFiles[i]->nppp, 116359599516SKenneth E. Jansen MPI_LONG_LONG_INT, 116459599516SKenneth E. Jansen header_table[j], 116559599516SKenneth E. Jansen PhastaIOActiveFiles[i]->nppp, 116659599516SKenneth E. Jansen MPI_LONG_LONG_INT, 116759599516SKenneth E. Jansen 0, 116859599516SKenneth E. Jansen PhastaIOActiveFiles[i]->local_comm ); 116959599516SKenneth E. Jansen } 117059599516SKenneth E. Jansen 117159599516SKenneth E. Jansen if ( PhastaIOActiveFiles[i]->local_myrank == 0 ) { 117259599516SKenneth E. Jansen 117359599516SKenneth E. Jansen //if( irank == 0 ) printf("gonna memcpy for every procs, myrank = %d\n", irank); 117459599516SKenneth E. Jansen for ( j = 0; j < PhastaIOActiveFiles[i]->nFields; j++ ) { 117559599516SKenneth E. Jansen memcpy ( PhastaIOActiveFiles[i]->master_header + 117659599516SKenneth E. Jansen VERSION_INFO_HEADER_SIZE + 11772dd307a1SCameron Smith j * PhastaIOActiveFiles[i]->nPPF * sizeof(unsigned long), 117859599516SKenneth E. Jansen header_table[j], 11792dd307a1SCameron Smith PhastaIOActiveFiles[i]->nPPF * sizeof(unsigned long) ); 118059599516SKenneth E. Jansen } 118159599516SKenneth E. Jansen 118259599516SKenneth E. Jansen //if( irank == 0 ) printf("gonna file_write_at(), myrank = %d\n", irank); 118359599516SKenneth E. Jansen MPI_File_write_at( PhastaIOActiveFiles[i]->file_handle, 118459599516SKenneth E. Jansen 0, 118559599516SKenneth E. Jansen PhastaIOActiveFiles[i]->master_header, 118659599516SKenneth E. Jansen MasterHeaderSize, 118759599516SKenneth E. Jansen MPI_CHAR, 118859599516SKenneth E. Jansen &write_header_status ); 118959599516SKenneth E. Jansen } 119059599516SKenneth E. Jansen 119159599516SKenneth E. Jansen ////free(PhastaIOActiveFiles[i]->master_header); 119259599516SKenneth E. Jansen 119359599516SKenneth E. Jansen for ( j = 0; j < PhastaIOActiveFiles[i]->nFields; j++ ) { 119459599516SKenneth E. Jansen free ( header_table[j] ); 119559599516SKenneth E. Jansen } 119659599516SKenneth E. Jansen free (header_table); 119759599516SKenneth E. Jansen } 119859599516SKenneth E. Jansen 119959599516SKenneth E. Jansen //if( irank == 0 ) printf("gonna file_close(), myrank = %d\n", irank); 120059599516SKenneth E. Jansen MPI_File_close( &( PhastaIOActiveFiles[i]->file_handle ) ); 120159599516SKenneth E. Jansen free ( imode ); 120259599516SKenneth E. Jansen } 120359599516SKenneth E. Jansen 120459599516SKenneth E. Jansen endTimer(&timer_end); 120559599516SKenneth E. Jansen printPerf("closefile_", timer_start, timer_end, 0, 0, ""); 120659599516SKenneth E. Jansen } 120759599516SKenneth E. Jansen 12083872e963SCameron Smith int readHeader( FILE* f, const char phrase[], 12093872e963SCameron Smith int* params, int numParams, const char* iotype) { 12103872e963SCameron Smith isBinary(iotype); 12113872e963SCameron Smith return readHeader(f,phrase,params,numParams); 12123872e963SCameron Smith } 12133872e963SCameron Smith 1214103be424SCameron Smith void readheader( 1215103be424SCameron Smith int* fileDescriptor, 121659599516SKenneth E. Jansen const char keyphrase[], 121759599516SKenneth E. Jansen void* valueArray, 121859599516SKenneth E. Jansen int* nItems, 121959599516SKenneth E. Jansen const char datatype[], 122059599516SKenneth E. Jansen const char iotype[] ) 122159599516SKenneth E. Jansen { 122259599516SKenneth E. Jansen double timer_start, timer_end; 1223d3337298SCameron Smith 122459599516SKenneth E. Jansen startTimer(&timer_start); 122559599516SKenneth E. Jansen 122659599516SKenneth E. Jansen int i = *fileDescriptor; 122759599516SKenneth E. Jansen checkFileDescriptor("readheader",&i); 122859599516SKenneth E. Jansen 122959599516SKenneth E. Jansen if ( PhastaIONextActiveIndex == 0 ) { 123059599516SKenneth E. Jansen int filePtr = *fileDescriptor - 1; 123159599516SKenneth E. Jansen FILE* fileObject; 123259599516SKenneth E. Jansen int* valueListInt; 123359599516SKenneth E. Jansen 123459599516SKenneth E. Jansen if ( *fileDescriptor < 1 || *fileDescriptor > (int)fileArray.size() ) { 123559599516SKenneth E. Jansen fprintf(stderr,"No file associated with Descriptor %d\n",*fileDescriptor); 123659599516SKenneth E. Jansen fprintf(stderr,"openfile_ function has to be called before \n") ; 123759599516SKenneth E. Jansen fprintf(stderr,"acessing the file\n ") ; 123859599516SKenneth E. Jansen fprintf(stderr,"fatal error: cannot continue, returning out of call\n"); 123959599516SKenneth E. Jansen endTimer(&timer_end); 124059599516SKenneth E. Jansen printPerf("readheader", timer_start, timer_end, 0, 0, ""); 124159599516SKenneth E. Jansen return; 124259599516SKenneth E. Jansen } 124359599516SKenneth E. Jansen 1244961a4ff6SCameron Smith LastHeaderKey[filePtr] = std::string(keyphrase); 124559599516SKenneth E. Jansen LastHeaderNotFound = false; 124659599516SKenneth E. Jansen 124759599516SKenneth E. Jansen fileObject = fileArray[ filePtr ] ; 124859599516SKenneth E. Jansen Wrong_Endian = byte_order[ filePtr ]; 124959599516SKenneth E. Jansen 125059599516SKenneth E. Jansen isBinary( iotype ); 125159599516SKenneth E. Jansen typeSize( datatype ); //redundant call, just avoid a compiler warning. 125259599516SKenneth E. Jansen 125359599516SKenneth E. Jansen // right now we are making the assumption that we will only write integers 125459599516SKenneth E. Jansen // on the header line. 125559599516SKenneth E. Jansen 125659599516SKenneth E. Jansen valueListInt = static_cast< int* >( valueArray ); 125759599516SKenneth E. Jansen int ierr = readHeader( fileObject , 125859599516SKenneth E. Jansen keyphrase, 125959599516SKenneth E. Jansen valueListInt, 126059599516SKenneth E. Jansen *nItems ) ; 126159599516SKenneth E. Jansen 126259599516SKenneth E. Jansen byte_order[ filePtr ] = Wrong_Endian ; 126359599516SKenneth E. Jansen 126459599516SKenneth E. Jansen if ( ierr ) LastHeaderNotFound = true; 126559599516SKenneth E. Jansen 126659599516SKenneth E. Jansen //return ; // don't return, go to the end to print perf 126759599516SKenneth E. Jansen } 126859599516SKenneth E. Jansen else { 126959599516SKenneth E. Jansen int* valueListInt; 127059599516SKenneth E. Jansen valueListInt = static_cast <int*>(valueArray); 1271400e9fc0SCameron Smith char* token = NULL; 127259599516SKenneth E. Jansen bool FOUND = false ; 127359599516SKenneth E. Jansen isBinary( iotype ); 127459599516SKenneth E. Jansen 127559599516SKenneth E. Jansen MPI_Status read_offset_status; 127659599516SKenneth E. Jansen char read_out_tag[MAX_FIELDS_NAME_LENGTH]; 1277400e9fc0SCameron Smith memset(read_out_tag, '\0', MAX_FIELDS_NAME_LENGTH); 127859599516SKenneth E. Jansen char readouttag[MAX_FIELDS_NUMBER][MAX_FIELDS_NAME_LENGTH]; 127959599516SKenneth E. Jansen int j; 128059599516SKenneth E. Jansen 128159599516SKenneth E. Jansen int string_length = strlen( keyphrase ); 128259599516SKenneth E. Jansen char* buffer = (char*) malloc ( string_length+1 ); 128359599516SKenneth E. Jansen 128459599516SKenneth E. Jansen strcpy ( buffer, keyphrase ); 128559599516SKenneth E. Jansen buffer[ string_length ] = '\0'; 128659599516SKenneth E. Jansen 128759599516SKenneth E. Jansen char* st2 = strtok ( buffer, "@" ); 128859599516SKenneth E. Jansen st2 = strtok (NULL, "@"); 128959599516SKenneth E. Jansen PhastaIOActiveFiles[i]->GPid = atoi(st2); 129059599516SKenneth E. Jansen if ( char* p = strpbrk(buffer, "@") ) 129159599516SKenneth E. Jansen *p = '\0'; 129259599516SKenneth E. Jansen 129359599516SKenneth E. Jansen // Check if the user has input the right GPid 129459599516SKenneth E. Jansen if ( ( PhastaIOActiveFiles[i]->GPid <= 129559599516SKenneth E. Jansen PhastaIOActiveFiles[i]->myrank * 129659599516SKenneth E. Jansen PhastaIOActiveFiles[i]->nppp )|| 129759599516SKenneth E. Jansen ( PhastaIOActiveFiles[i]->GPid > 129859599516SKenneth E. Jansen ( PhastaIOActiveFiles[i]->myrank + 1 ) * 129959599516SKenneth E. Jansen PhastaIOActiveFiles[i]->nppp ) ) 130059599516SKenneth E. Jansen { 130159599516SKenneth E. Jansen *fileDescriptor = NOT_A_MPI_FILE; 130259599516SKenneth E. Jansen printf("Error readheader: The file is not in syncIO new format, please check! myrank = %d, GPid = %d, nppp = %d, keyphrase = %s\n", PhastaIOActiveFiles[i]->myrank, PhastaIOActiveFiles[i]->GPid, PhastaIOActiveFiles[i]->nppp, keyphrase); 130359599516SKenneth E. Jansen // It is possible atoi could not generate a clear integer from st2 because of additional garbage character in keyphrase 130459599516SKenneth E. Jansen endTimer(&timer_end); 130559599516SKenneth E. Jansen printPerf("readheader", timer_start, timer_end, 0, 0, ""); 130659599516SKenneth E. Jansen return; 130759599516SKenneth E. Jansen } 130859599516SKenneth E. Jansen 130959599516SKenneth E. Jansen // Find the field we want ... 131059599516SKenneth E. Jansen //for ( j = 0; j<MAX_FIELDS_NUMBER; j++ ) 131159599516SKenneth E. Jansen for ( j = 0; j<PhastaIOActiveFiles[i]->nFields; j++ ) 131259599516SKenneth E. Jansen { 131359599516SKenneth E. Jansen memcpy( readouttag[j], 131459599516SKenneth E. Jansen PhastaIOActiveFiles[i]->master_header + j*MAX_FIELDS_NAME_LENGTH+MAX_FIELDS_NAME_LENGTH*2+1, 131559599516SKenneth E. Jansen MAX_FIELDS_NAME_LENGTH-1 ); 131659599516SKenneth E. Jansen } 131759599516SKenneth E. Jansen 131859599516SKenneth E. Jansen for ( j = 0; j<PhastaIOActiveFiles[i]->nFields; j++ ) 131959599516SKenneth E. Jansen { 132059599516SKenneth E. Jansen token = strtok ( readouttag[j], ":" ); 132159599516SKenneth E. Jansen 132259599516SKenneth E. Jansen //if ( cscompare( buffer, token ) ) 132359599516SKenneth E. Jansen if ( cscompare( token , buffer ) && cscompare( buffer, token ) ) 132459599516SKenneth E. Jansen // This double comparison is required for the field "number of nodes" and all the other fields that start with "number of nodes" (i.g. number of nodes in the mesh"). 132559599516SKenneth E. Jansen // Would be safer to rename "number of nodes" by "number of nodes in the part" so that the name are completely unique. But much more work to do that (Nspre, phParAdapt, etc). 132659599516SKenneth E. Jansen // Since the field name are unique in SyncIO (as it includes part ID), this should be safe and there should be no issue with the "?" trailing character. 132759599516SKenneth E. Jansen { 132859599516SKenneth E. Jansen PhastaIOActiveFiles[i]->read_field_count = j; 132959599516SKenneth E. Jansen FOUND = true; 133059599516SKenneth E. Jansen //printf("buffer: %s | token: %s | j: %d\n",buffer,token,j); 133159599516SKenneth E. Jansen break; 133259599516SKenneth E. Jansen } 133359599516SKenneth E. Jansen } 133459599516SKenneth E. Jansen free(buffer); 133559599516SKenneth E. Jansen 133659599516SKenneth E. Jansen if (!FOUND) 133759599516SKenneth E. Jansen { 133859599516SKenneth E. Jansen //if(irank==0) printf("Warning readheader: Not found %s \n",keyphrase); //PhastaIOActiveFiles[i]->myrank is certainly initialized here. 133959599516SKenneth E. Jansen if(PhastaIOActiveFiles[i]->myrank == 0) printf("WARNING readheader: Not found %s\n",keyphrase); 134059599516SKenneth E. Jansen endTimer(&timer_end); 134159599516SKenneth E. Jansen printPerf("readheader", timer_start, timer_end, 0, 0, ""); 134259599516SKenneth E. Jansen return; 134359599516SKenneth E. Jansen } 134459599516SKenneth E. Jansen 134559599516SKenneth E. Jansen // Find the part we want ... 134659599516SKenneth E. Jansen PhastaIOActiveFiles[i]->read_part_count = PhastaIOActiveFiles[i]->GPid - 134759599516SKenneth E. Jansen PhastaIOActiveFiles[i]->myrank * PhastaIOActiveFiles[i]->nppp - 1; 134859599516SKenneth E. Jansen 134959599516SKenneth E. Jansen PhastaIOActiveFiles[i]->my_offset = 135059599516SKenneth E. Jansen PhastaIOActiveFiles[i]->my_read_table[PhastaIOActiveFiles[i]->read_field_count][PhastaIOActiveFiles[i]->read_part_count]; 135159599516SKenneth E. Jansen 135259599516SKenneth E. Jansen // printf("****Rank %d offset is %d\n",PhastaIOActiveFiles[i]->myrank,PhastaIOActiveFiles[i]->my_offset); 135359599516SKenneth E. Jansen 135459599516SKenneth E. Jansen // Read each datablock header here ... 135559599516SKenneth E. Jansen 135659599516SKenneth E. Jansen MPI_File_read_at_all( PhastaIOActiveFiles[i]->file_handle, 135759599516SKenneth E. Jansen PhastaIOActiveFiles[i]->my_offset+1, 135859599516SKenneth E. Jansen read_out_tag, 135959599516SKenneth E. Jansen MAX_FIELDS_NAME_LENGTH-1, 136059599516SKenneth E. Jansen MPI_CHAR, 136159599516SKenneth E. Jansen &read_offset_status ); 136259599516SKenneth E. Jansen token = strtok ( read_out_tag, ":" ); 136359599516SKenneth E. Jansen 136459599516SKenneth E. Jansen // printf("&&&&Rank %d read_out_tag is %s\n",PhastaIOActiveFiles[i]->myrank,read_out_tag); 136559599516SKenneth E. Jansen 136659599516SKenneth E. Jansen if( cscompare( keyphrase , token ) ) //No need to compare also token with keyphrase like above. We should already have the right one. Otherwise there is a problem. 136759599516SKenneth E. Jansen { 136859599516SKenneth E. Jansen FOUND = true ; 136959599516SKenneth E. Jansen token = strtok( NULL, " ,;<>" ); 137059599516SKenneth E. Jansen for( j=0; j < *nItems && ( token = strtok( NULL," ,;<>") ); j++ ) 137159599516SKenneth E. Jansen valueListInt[j] = atoi( token ); 137259599516SKenneth E. Jansen 137359599516SKenneth E. Jansen if ( j < *nItems ) 137459599516SKenneth E. Jansen { 137559599516SKenneth E. Jansen fprintf( stderr, "Expected # of ints not found for: %s\n", keyphrase ); 137659599516SKenneth E. Jansen } 137759599516SKenneth E. Jansen } 137859599516SKenneth E. Jansen else { 137959599516SKenneth E. Jansen //if(irank==0) 138059599516SKenneth E. Jansen if(PhastaIOActiveFiles[i]->myrank == 0) 138159599516SKenneth E. Jansen // If we enter this if, there is a problem with the name of some fields 138259599516SKenneth E. Jansen { 138359599516SKenneth E. Jansen printf("Error readheader: Unexpected mismatch between keyphrase = %s and token = %s\n",keyphrase,token); 138459599516SKenneth E. Jansen } 138559599516SKenneth E. Jansen } 138659599516SKenneth E. Jansen } 138759599516SKenneth E. Jansen 138859599516SKenneth E. Jansen endTimer(&timer_end); 138959599516SKenneth E. Jansen printPerf("readheader", timer_start, timer_end, 0, 0, ""); 139059599516SKenneth E. Jansen 139159599516SKenneth E. Jansen } 139259599516SKenneth E. Jansen 13933956dcfeSCameron Smith void readDataBlock( 13943956dcfeSCameron Smith FILE* fileObject, 13953956dcfeSCameron Smith void* valueArray, 13963956dcfeSCameron Smith int nItems, 13973956dcfeSCameron Smith const char datatype[], 13983956dcfeSCameron Smith const char iotype[] ) 13993956dcfeSCameron Smith { 14003956dcfeSCameron Smith isBinary(iotype); 14013956dcfeSCameron Smith size_t type_size = typeSize( datatype ); 14023956dcfeSCameron Smith if ( binary_format ) { 14033956dcfeSCameron Smith char junk = '\0'; 14043956dcfeSCameron Smith fread( valueArray, type_size, nItems, fileObject ); 14053956dcfeSCameron Smith fread( &junk, sizeof(char), 1 , fileObject ); 14063956dcfeSCameron Smith if ( Wrong_Endian ) SwapArrayByteOrder( valueArray, type_size, nItems ); 14073956dcfeSCameron Smith } else { 14083956dcfeSCameron Smith char* ts1 = StringStripper( datatype ); 14093956dcfeSCameron Smith if ( cscompare( "integer", ts1 ) ) { 14103956dcfeSCameron Smith for( int n=0; n < nItems ; n++ ) 14113956dcfeSCameron Smith fscanf(fileObject, "%d\n",(int*)((int*)valueArray+n) ); 14123956dcfeSCameron Smith } else if ( cscompare( "double", ts1 ) ) { 14133956dcfeSCameron Smith for( int n=0; n < nItems ; n++ ) 14143956dcfeSCameron Smith fscanf(fileObject, "%lf\n",(double*)((double*)valueArray+n) ); 14153956dcfeSCameron Smith } 14163956dcfeSCameron Smith free (ts1); 14173956dcfeSCameron Smith } 14183956dcfeSCameron Smith } 14193956dcfeSCameron Smith 1420103be424SCameron Smith void readdatablock( 1421103be424SCameron Smith int* fileDescriptor, 142259599516SKenneth E. Jansen const char keyphrase[], 142359599516SKenneth E. Jansen void* valueArray, 142459599516SKenneth E. Jansen int* nItems, 142559599516SKenneth E. Jansen const char datatype[], 142659599516SKenneth E. Jansen const char iotype[] ) 142759599516SKenneth E. Jansen { 142859599516SKenneth E. Jansen //if(irank == 0) printf("entering readdatablock()\n"); 14292dd307a1SCameron Smith unsigned long data_size = 0; 143059599516SKenneth E. Jansen double timer_start, timer_end; 143159599516SKenneth E. Jansen startTimer(&timer_start); 143259599516SKenneth E. Jansen 143359599516SKenneth E. Jansen int i = *fileDescriptor; 143459599516SKenneth E. Jansen checkFileDescriptor("readdatablock",&i); 143559599516SKenneth E. Jansen 143659599516SKenneth E. Jansen if ( PhastaIONextActiveIndex == 0 ) { 143759599516SKenneth E. Jansen int filePtr = *fileDescriptor - 1; 143859599516SKenneth E. Jansen FILE* fileObject; 143959599516SKenneth E. Jansen 144059599516SKenneth E. Jansen if ( *fileDescriptor < 1 || *fileDescriptor > (int)fileArray.size() ) { 144159599516SKenneth E. Jansen fprintf(stderr,"No file associated with Descriptor %d\n",*fileDescriptor); 144259599516SKenneth E. Jansen fprintf(stderr,"openfile_ function has to be called before\n") ; 144359599516SKenneth E. Jansen fprintf(stderr,"acessing the file\n ") ; 144459599516SKenneth E. Jansen fprintf(stderr,"fatal error: cannot continue, returning out of call\n"); 144559599516SKenneth E. Jansen endTimer(&timer_end); 144659599516SKenneth E. Jansen printPerf("readdatablock", timer_start, timer_end, 0, 0, ""); 144759599516SKenneth E. Jansen return; 144859599516SKenneth E. Jansen } 144959599516SKenneth E. Jansen 145059599516SKenneth E. Jansen // error check.. 145159599516SKenneth E. Jansen // since we require that a consistant header always preceed the data block 145259599516SKenneth E. Jansen // let us check to see that it is actually the case. 145359599516SKenneth E. Jansen 1454961a4ff6SCameron Smith if ( ! cscompare( LastHeaderKey[ filePtr ].c_str(), keyphrase ) ) { 145559599516SKenneth E. Jansen fprintf(stderr, "Header not consistant with data block\n"); 1456961a4ff6SCameron Smith fprintf(stderr, "Header: %s\n", LastHeaderKey[ filePtr ].c_str() ); 145759599516SKenneth E. Jansen fprintf(stderr, "DataBlock: %s\n ", keyphrase ); 145859599516SKenneth E. Jansen fprintf(stderr, "Please recheck read sequence \n"); 145959599516SKenneth E. Jansen if( Strict_Error ) { 146059599516SKenneth E. Jansen fprintf(stderr, "fatal error: cannot continue, returning out of call\n"); 146159599516SKenneth E. Jansen endTimer(&timer_end); 146259599516SKenneth E. Jansen printPerf("readdatablock", timer_start, timer_end, 0, 0, ""); 146359599516SKenneth E. Jansen return; 146459599516SKenneth E. Jansen } 146559599516SKenneth E. Jansen } 146659599516SKenneth E. Jansen 146759599516SKenneth E. Jansen if ( LastHeaderNotFound ) { 146859599516SKenneth E. Jansen endTimer(&timer_end); 146959599516SKenneth E. Jansen printPerf("readdatablock", timer_start, timer_end, 0, 0, ""); 147059599516SKenneth E. Jansen return; 147159599516SKenneth E. Jansen } 147259599516SKenneth E. Jansen fileObject = fileArray[ filePtr ]; 147359599516SKenneth E. Jansen Wrong_Endian = byte_order[ filePtr ]; 1474bae968b9SCameron Smith LastHeaderKey.erase(filePtr); 14753956dcfeSCameron Smith readDataBlock(fileObject,valueArray,*nItems,datatype,iotype); 147659599516SKenneth E. Jansen 147759599516SKenneth E. Jansen //return; 147859599516SKenneth E. Jansen } 147959599516SKenneth E. Jansen else { 148059599516SKenneth E. Jansen // printf("read data block\n"); 148159599516SKenneth E. Jansen MPI_Status read_data_status; 148259599516SKenneth E. Jansen size_t type_size = typeSize( datatype ); 148359599516SKenneth E. Jansen int nUnits = *nItems; 148459599516SKenneth E. Jansen isBinary( iotype ); 148559599516SKenneth E. Jansen 148659599516SKenneth E. Jansen // read datablock then 148759599516SKenneth E. Jansen //MR CHANGE 148859599516SKenneth E. Jansen // if ( cscompare ( datatype, "double")) 148959599516SKenneth E. Jansen char* ts2 = StringStripper( datatype ); 149059599516SKenneth E. Jansen if ( cscompare ( "double" , ts2)) 149159599516SKenneth E. Jansen //MR CHANGE END 149259599516SKenneth E. Jansen { 149359599516SKenneth E. Jansen 149459599516SKenneth E. Jansen MPI_File_read_at_all_begin( PhastaIOActiveFiles[i]->file_handle, 149559599516SKenneth E. Jansen PhastaIOActiveFiles[i]->my_offset + DB_HEADER_SIZE, 149659599516SKenneth E. Jansen valueArray, 149759599516SKenneth E. Jansen nUnits, 149859599516SKenneth E. Jansen MPI_DOUBLE ); 149959599516SKenneth E. Jansen MPI_File_read_at_all_end( PhastaIOActiveFiles[i]->file_handle, 150059599516SKenneth E. Jansen valueArray, 150159599516SKenneth E. Jansen &read_data_status ); 150259599516SKenneth E. Jansen data_size=8*nUnits; 150359599516SKenneth E. Jansen 150459599516SKenneth E. Jansen } 150559599516SKenneth E. Jansen //MR CHANGE 150659599516SKenneth E. Jansen // else if ( cscompare ( datatype, "integer")) 150759599516SKenneth E. Jansen else if ( cscompare ( "integer" , ts2)) 150859599516SKenneth E. Jansen //MR CHANGE END 150959599516SKenneth E. Jansen { 151059599516SKenneth E. Jansen MPI_File_read_at_all_begin(PhastaIOActiveFiles[i]->file_handle, 151159599516SKenneth E. Jansen PhastaIOActiveFiles[i]->my_offset + DB_HEADER_SIZE, 151259599516SKenneth E. Jansen valueArray, 151359599516SKenneth E. Jansen nUnits, 151459599516SKenneth E. Jansen MPI_INT ); 151559599516SKenneth E. Jansen MPI_File_read_at_all_end( PhastaIOActiveFiles[i]->file_handle, 151659599516SKenneth E. Jansen valueArray, 151759599516SKenneth E. Jansen &read_data_status ); 151859599516SKenneth E. Jansen data_size=4*nUnits; 151959599516SKenneth E. Jansen } 152059599516SKenneth E. Jansen else 152159599516SKenneth E. Jansen { 152259599516SKenneth E. Jansen *fileDescriptor = DATA_TYPE_ILLEGAL; 152359599516SKenneth E. Jansen printf("readdatablock - DATA_TYPE_ILLEGAL - %s\n",datatype); 152459599516SKenneth E. Jansen endTimer(&timer_end); 152559599516SKenneth E. Jansen printPerf("readdatablock", timer_start, timer_end, 0, 0, ""); 152659599516SKenneth E. Jansen return; 152759599516SKenneth E. Jansen } 152859599516SKenneth E. Jansen free(ts2); 152959599516SKenneth E. Jansen 153059599516SKenneth E. Jansen 153159599516SKenneth E. Jansen // printf("%d Read finishe\n",PhastaIOActiveFiles[i]->myrank); 153259599516SKenneth E. Jansen 153359599516SKenneth E. Jansen // Swap data byte order if endianess is different ... 153459599516SKenneth E. Jansen if ( PhastaIOActiveFiles[i]->Wrong_Endian ) 153559599516SKenneth E. Jansen { 153659599516SKenneth E. Jansen SwapArrayByteOrder( valueArray, type_size, nUnits ); 153759599516SKenneth E. Jansen } 153859599516SKenneth E. Jansen } 153959599516SKenneth E. Jansen 154059599516SKenneth E. Jansen endTimer(&timer_end); 154159599516SKenneth E. Jansen char extra_msg[1024]; 154259599516SKenneth E. Jansen memset(extra_msg, '\0', 1024); 154359599516SKenneth E. Jansen char* key = StringStripper(keyphrase); 154459599516SKenneth E. Jansen sprintf(extra_msg, " field is %s ", key); 154559599516SKenneth E. Jansen printPerf("readdatablock", timer_start, timer_end, data_size, 1, extra_msg); 154659599516SKenneth E. Jansen free(key); 154759599516SKenneth E. Jansen 154859599516SKenneth E. Jansen } 154959599516SKenneth E. Jansen 1550103be424SCameron Smith void writeHeader( 1551103be424SCameron Smith FILE* f, 1552ea868eb1SCameron Smith const char keyphrase[], 1553ea868eb1SCameron Smith const void* valueArray, 1554ea868eb1SCameron Smith const int nItems, 1555ea868eb1SCameron Smith const int ndataItems, 1556ea868eb1SCameron Smith const char datatype[], 1557ea868eb1SCameron Smith const char iotype[]) 1558ea868eb1SCameron Smith { 1559ea868eb1SCameron Smith isBinary( iotype ); 1560ea868eb1SCameron Smith 1561ea868eb1SCameron Smith const int _newline = 1562ea868eb1SCameron Smith ( ndataItems > 0 ) ? sizeof( char ) : 0; 1563ea868eb1SCameron Smith int size_of_nextblock = 1564ea868eb1SCameron Smith ( binary_format ) ? typeSize(datatype) * ndataItems + _newline : ndataItems; 1565ea868eb1SCameron Smith 1566ea868eb1SCameron Smith fprintf( f, "%s : < %d > ", keyphrase, size_of_nextblock ); 1567ea868eb1SCameron Smith for( int i = 0; i < nItems; i++ ) 1568ea868eb1SCameron Smith fprintf( f, "%d ", *((int*)((int*)valueArray+i))); 1569ea868eb1SCameron Smith fprintf( f, "\n"); 1570ea868eb1SCameron Smith } 1571ea868eb1SCameron Smith 1572103be424SCameron Smith void writeheader( 1573103be424SCameron Smith const int* fileDescriptor, 157459599516SKenneth E. Jansen const char keyphrase[], 157559599516SKenneth E. Jansen const void* valueArray, 157659599516SKenneth E. Jansen const int* nItems, 157759599516SKenneth E. Jansen const int* ndataItems, 157859599516SKenneth E. Jansen const char datatype[], 157959599516SKenneth E. Jansen const char iotype[]) 158059599516SKenneth E. Jansen { 158159599516SKenneth E. Jansen 158259599516SKenneth E. Jansen //if(irank == 0) printf("entering writeheader()\n"); 158359599516SKenneth E. Jansen 158459599516SKenneth E. Jansen double timer_start, timer_end; 158559599516SKenneth E. Jansen startTimer(&timer_start); 158659599516SKenneth E. Jansen 158759599516SKenneth E. Jansen int i = *fileDescriptor; 158859599516SKenneth E. Jansen checkFileDescriptor("writeheader",&i); 158959599516SKenneth E. Jansen 159059599516SKenneth E. Jansen if ( PhastaIONextActiveIndex == 0 ) { 159159599516SKenneth E. Jansen int filePtr = *fileDescriptor - 1; 159259599516SKenneth E. Jansen if ( *fileDescriptor < 1 || *fileDescriptor > (int)fileArray.size() ) { 159359599516SKenneth E. Jansen fprintf(stderr,"No file associated with Descriptor %d\n",*fileDescriptor); 159459599516SKenneth E. Jansen fprintf(stderr,"openfile_ function has to be called before \n") ; 159559599516SKenneth E. Jansen fprintf(stderr,"acessing the file\n ") ; 159659599516SKenneth E. Jansen fprintf(stderr,"fatal error: cannot continue, returning out of call\n"); 159759599516SKenneth E. Jansen endTimer(&timer_end); 159859599516SKenneth E. Jansen printPerf("writeheader", timer_start, timer_end, 0, 0, ""); 159959599516SKenneth E. Jansen return; 160059599516SKenneth E. Jansen } 160159599516SKenneth E. Jansen 1602961a4ff6SCameron Smith LastHeaderKey[filePtr] = std::string(keyphrase); 160359599516SKenneth E. Jansen DataSize = *ndataItems; 1604ea868eb1SCameron Smith FILE* fileObject = fileArray[ filePtr ] ; 1605ea868eb1SCameron Smith header_type[ filePtr ] = typeSize( datatype ); 1606ea868eb1SCameron Smith writeHeader(fileObject,keyphrase,valueArray,*nItems, 1607ea868eb1SCameron Smith *ndataItems,datatype,iotype); 160859599516SKenneth E. Jansen } 160959599516SKenneth E. Jansen else { // else it's parallel I/O 161059599516SKenneth E. Jansen DataSize = *ndataItems; 161159599516SKenneth E. Jansen size_t type_size = typeSize( datatype ); 161259599516SKenneth E. Jansen isBinary( iotype ); 161359599516SKenneth E. Jansen char mpi_tag[MAX_FIELDS_NAME_LENGTH]; 161459599516SKenneth E. Jansen 161559599516SKenneth E. Jansen int string_length = strlen( keyphrase ); 161659599516SKenneth E. Jansen char* buffer = (char*) malloc ( string_length+1 ); 161759599516SKenneth E. Jansen 161859599516SKenneth E. Jansen strcpy ( buffer, keyphrase); 161959599516SKenneth E. Jansen buffer[ string_length ] = '\0'; 162059599516SKenneth E. Jansen 162159599516SKenneth E. Jansen char* st2 = strtok ( buffer, "@" ); 162259599516SKenneth E. Jansen st2 = strtok (NULL, "@"); 162359599516SKenneth E. Jansen PhastaIOActiveFiles[i]->GPid = atoi(st2); 162459599516SKenneth E. Jansen 162559599516SKenneth E. Jansen if ( char* p = strpbrk(buffer, "@") ) 162659599516SKenneth E. Jansen *p = '\0'; 162759599516SKenneth E. Jansen 162859599516SKenneth E. Jansen bzero((void*)mpi_tag,MAX_FIELDS_NAME_LENGTH); 162959599516SKenneth E. Jansen sprintf(mpi_tag, "\n%s : %d\n", buffer, PhastaIOActiveFiles[i]->field_count); 16302dd307a1SCameron Smith unsigned long offset_value; 163159599516SKenneth E. Jansen 163259599516SKenneth E. Jansen int temp = *ndataItems; 16332dd307a1SCameron Smith unsigned long number_of_items = (unsigned long)temp; 163459599516SKenneth E. Jansen MPI_Barrier(PhastaIOActiveFiles[i]->local_comm); 163559599516SKenneth E. Jansen 163659599516SKenneth E. Jansen MPI_Scan( &number_of_items, 163759599516SKenneth E. Jansen &offset_value, 163859599516SKenneth E. Jansen 1, 163959599516SKenneth E. Jansen MPI_LONG_LONG_INT, 164059599516SKenneth E. Jansen MPI_SUM, 164159599516SKenneth E. Jansen PhastaIOActiveFiles[i]->local_comm ); 164259599516SKenneth E. Jansen 164359599516SKenneth E. Jansen offset_value = (offset_value - number_of_items) * type_size; 164459599516SKenneth E. Jansen 164559599516SKenneth E. Jansen offset_value += PhastaIOActiveFiles[i]->local_myrank * 164659599516SKenneth E. Jansen DB_HEADER_SIZE + 164759599516SKenneth E. Jansen PhastaIOActiveFiles[i]->next_start_address; 164859599516SKenneth E. Jansen // This offset is the starting address of each datablock header... 164959599516SKenneth E. Jansen PhastaIOActiveFiles[i]->my_offset = offset_value; 165059599516SKenneth E. Jansen 165159599516SKenneth E. Jansen // Write in my offset table ... 165259599516SKenneth E. Jansen PhastaIOActiveFiles[i]->my_offset_table[PhastaIOActiveFiles[i]->field_count][PhastaIOActiveFiles[i]->part_count] = 165359599516SKenneth E. Jansen PhastaIOActiveFiles[i]->my_offset; 165459599516SKenneth E. Jansen 165559599516SKenneth E. Jansen // Update the next-start-address ... 165659599516SKenneth E. Jansen PhastaIOActiveFiles[i]->next_start_address = offset_value + 165759599516SKenneth E. Jansen number_of_items * type_size + 165859599516SKenneth E. Jansen DB_HEADER_SIZE; 165959599516SKenneth E. Jansen MPI_Bcast( &(PhastaIOActiveFiles[i]->next_start_address), 166059599516SKenneth E. Jansen 1, 166159599516SKenneth E. Jansen MPI_LONG_LONG_INT, 166259599516SKenneth E. Jansen PhastaIOActiveFiles[i]->local_numprocs-1, 166359599516SKenneth E. Jansen PhastaIOActiveFiles[i]->local_comm ); 166459599516SKenneth E. Jansen 166559599516SKenneth E. Jansen // Prepare datablock header ... 166659599516SKenneth E. Jansen int _newline = (*ndataItems>0)?sizeof(char):0; 166759599516SKenneth E. Jansen unsigned int size_of_nextblock = type_size * (*ndataItems) + _newline; 166859599516SKenneth E. Jansen 166959599516SKenneth E. Jansen //char datablock_header[255]; 167059599516SKenneth E. Jansen //bzero((void*)datablock_header,255); 167159599516SKenneth E. Jansen char datablock_header[DB_HEADER_SIZE]; 167259599516SKenneth E. Jansen bzero((void*)datablock_header,DB_HEADER_SIZE); 167359599516SKenneth E. Jansen 167459599516SKenneth E. Jansen PhastaIOActiveFiles[i]->GPid = PhastaIOActiveFiles[i]->nppp*PhastaIOActiveFiles[i]->myrank+PhastaIOActiveFiles[i]->part_count; 167559599516SKenneth E. Jansen sprintf( datablock_header, 167659599516SKenneth E. Jansen "\n%s : < %u >", 167759599516SKenneth E. Jansen keyphrase, 167859599516SKenneth E. Jansen size_of_nextblock ); 167959599516SKenneth E. Jansen 168059599516SKenneth E. Jansen for ( int j = 0; j < *nItems; j++ ) 168159599516SKenneth E. Jansen { 168259599516SKenneth E. Jansen sprintf( datablock_header, 168359599516SKenneth E. Jansen "%s %d ", 168459599516SKenneth E. Jansen datablock_header, 168559599516SKenneth E. Jansen *((int*)((int*)valueArray+j))); 168659599516SKenneth E. Jansen } 168759599516SKenneth E. Jansen sprintf( datablock_header, 168859599516SKenneth E. Jansen "%s\n ", 168959599516SKenneth E. Jansen datablock_header ); 169059599516SKenneth E. Jansen 169159599516SKenneth E. Jansen // Write datablock header ... 169259599516SKenneth E. Jansen //MR CHANGE 169359599516SKenneth E. Jansen // if ( cscompare(datatype,"double") ) 169459599516SKenneth E. Jansen char* ts1 = StringStripper( datatype ); 169559599516SKenneth E. Jansen if ( cscompare("double",ts1) ) 169659599516SKenneth E. Jansen //MR CHANGE END 169759599516SKenneth E. Jansen { 169859599516SKenneth E. Jansen free ( PhastaIOActiveFiles[i]->double_chunk ); 169959599516SKenneth E. Jansen PhastaIOActiveFiles[i]->double_chunk = ( double * )malloc( (sizeof( double )*number_of_items+ DB_HEADER_SIZE)); 170059599516SKenneth E. Jansen 170159599516SKenneth E. Jansen double * aa = ( double * )datablock_header; 170259599516SKenneth E. Jansen memcpy(PhastaIOActiveFiles[i]->double_chunk, aa, DB_HEADER_SIZE); 170359599516SKenneth E. Jansen } 170459599516SKenneth E. Jansen //MR CHANGE 170559599516SKenneth E. Jansen // if ( cscompare(datatype,"integer") ) 170659599516SKenneth E. Jansen else if ( cscompare("integer",ts1) ) 170759599516SKenneth E. Jansen //MR CHANGE END 170859599516SKenneth E. Jansen { 170959599516SKenneth E. Jansen free ( PhastaIOActiveFiles[i]->int_chunk ); 171059599516SKenneth E. Jansen PhastaIOActiveFiles[i]->int_chunk = ( int * )malloc( (sizeof( int )*number_of_items+ DB_HEADER_SIZE)); 171159599516SKenneth E. Jansen 171259599516SKenneth E. Jansen int * aa = ( int * )datablock_header; 171359599516SKenneth E. Jansen memcpy(PhastaIOActiveFiles[i]->int_chunk, aa, DB_HEADER_SIZE); 171459599516SKenneth E. Jansen } 171559599516SKenneth E. Jansen else { 171659599516SKenneth E. Jansen // *fileDescriptor = DATA_TYPE_ILLEGAL; 171759599516SKenneth E. Jansen printf("writeheader - DATA_TYPE_ILLEGAL - %s\n",datatype); 171859599516SKenneth E. Jansen endTimer(&timer_end); 171959599516SKenneth E. Jansen printPerf("writeheader", timer_start, timer_end, 0, 0, ""); 172059599516SKenneth E. Jansen return; 172159599516SKenneth E. Jansen } 172259599516SKenneth E. Jansen free(ts1); 172359599516SKenneth E. Jansen 172459599516SKenneth E. Jansen PhastaIOActiveFiles[i]->part_count++; 172559599516SKenneth E. Jansen if ( PhastaIOActiveFiles[i]->part_count == PhastaIOActiveFiles[i]->nppp ) { 172659599516SKenneth E. Jansen //A new field will be written 172759599516SKenneth E. Jansen if ( PhastaIOActiveFiles[i]->local_myrank == 0 ) { 172859599516SKenneth E. Jansen memcpy( PhastaIOActiveFiles[i]->master_header + 172959599516SKenneth E. Jansen PhastaIOActiveFiles[i]->field_count * 173059599516SKenneth E. Jansen MAX_FIELDS_NAME_LENGTH + 173159599516SKenneth E. Jansen MAX_FIELDS_NAME_LENGTH * 2, 173259599516SKenneth E. Jansen mpi_tag, 173359599516SKenneth E. Jansen MAX_FIELDS_NAME_LENGTH-1); 173459599516SKenneth E. Jansen } 173559599516SKenneth E. Jansen PhastaIOActiveFiles[i]->field_count++; 173659599516SKenneth E. Jansen PhastaIOActiveFiles[i]->part_count=0; 173759599516SKenneth E. Jansen } 173859599516SKenneth E. Jansen free(buffer); 173959599516SKenneth E. Jansen } 174059599516SKenneth E. Jansen 174159599516SKenneth E. Jansen endTimer(&timer_end); 174259599516SKenneth E. Jansen printPerf("writeheader", timer_start, timer_end, 0, 0, ""); 174359599516SKenneth E. Jansen } 174459599516SKenneth E. Jansen 1745103be424SCameron Smith void writeDataBlock( 1746103be424SCameron Smith FILE* f, 1747ea868eb1SCameron Smith const void* valueArray, 1748ea868eb1SCameron Smith const int nItems, 1749ea868eb1SCameron Smith const char datatype[], 1750ea868eb1SCameron Smith const char iotype[] ) 1751ea868eb1SCameron Smith { 1752ea868eb1SCameron Smith isBinary( iotype ); 1753ea868eb1SCameron Smith size_t type_size = typeSize( datatype ); 1754ea868eb1SCameron Smith if ( binary_format ) { 1755ea868eb1SCameron Smith fwrite( valueArray, type_size, nItems, f ); 1756ea868eb1SCameron Smith fprintf( f,"\n"); 1757ea868eb1SCameron Smith } else { 1758ea868eb1SCameron Smith char* ts1 = StringStripper( datatype ); 1759ea868eb1SCameron Smith if ( cscompare( "integer", ts1 ) ) { 1760be3da47bSCameron Smith const int* vals = (int*) valueArray; 1761ea868eb1SCameron Smith for( int n=0; n < nItems ; n++ ) 1762be3da47bSCameron Smith fprintf(f,"%d\n",vals[n]); 1763ea868eb1SCameron Smith } else if ( cscompare( "double", ts1 ) ) { 1764be3da47bSCameron Smith const double* vals = (double*) valueArray; 1765ea868eb1SCameron Smith for( int n=0; n < nItems ; n++ ) 1766be3da47bSCameron Smith fprintf(f,"%f\n",vals[n]); 1767ea868eb1SCameron Smith } 1768ea868eb1SCameron Smith free (ts1); 1769ea868eb1SCameron Smith } 1770ea868eb1SCameron Smith } 1771ea868eb1SCameron Smith 1772103be424SCameron Smith void writedatablock( 1773103be424SCameron Smith const int* fileDescriptor, 177459599516SKenneth E. Jansen const char keyphrase[], 177559599516SKenneth E. Jansen const void* valueArray, 177659599516SKenneth E. Jansen const int* nItems, 177759599516SKenneth E. Jansen const char datatype[], 177859599516SKenneth E. Jansen const char iotype[] ) 177959599516SKenneth E. Jansen { 178059599516SKenneth E. Jansen //if(irank == 0) printf("entering writedatablock()\n"); 178159599516SKenneth E. Jansen 17822dd307a1SCameron Smith unsigned long data_size = 0; 178359599516SKenneth E. Jansen double timer_start, timer_end; 178459599516SKenneth E. Jansen startTimer(&timer_start); 178559599516SKenneth E. Jansen 178659599516SKenneth E. Jansen int i = *fileDescriptor; 178759599516SKenneth E. Jansen checkFileDescriptor("writedatablock",&i); 178859599516SKenneth E. Jansen 178959599516SKenneth E. Jansen if ( PhastaIONextActiveIndex == 0 ) { 179059599516SKenneth E. Jansen int filePtr = *fileDescriptor - 1; 179159599516SKenneth E. Jansen 179259599516SKenneth E. Jansen if ( *fileDescriptor < 1 || *fileDescriptor > (int)fileArray.size() ) { 179359599516SKenneth E. Jansen fprintf(stderr,"No file associated with Descriptor %d\n",*fileDescriptor); 179459599516SKenneth E. Jansen fprintf(stderr,"openfile_ function has to be called before \n") ; 179559599516SKenneth E. Jansen fprintf(stderr,"acessing the file\n ") ; 179659599516SKenneth E. Jansen fprintf(stderr,"fatal error: cannot continue, returning out of call\n"); 179759599516SKenneth E. Jansen endTimer(&timer_end); 179859599516SKenneth E. Jansen printPerf("writedatablock", timer_start, timer_end, 0, 0, ""); 179959599516SKenneth E. Jansen return; 180059599516SKenneth E. Jansen } 180159599516SKenneth E. Jansen // since we require that a consistant header always preceed the data block 180259599516SKenneth E. Jansen // let us check to see that it is actually the case. 180359599516SKenneth E. Jansen 1804961a4ff6SCameron Smith if ( ! cscompare( LastHeaderKey[ filePtr ].c_str(), keyphrase ) ) { 180559599516SKenneth E. Jansen fprintf(stderr, "Header not consistant with data block\n"); 1806961a4ff6SCameron Smith fprintf(stderr, "Header: %s\n", LastHeaderKey[ filePtr ].c_str() ); 180759599516SKenneth E. Jansen fprintf(stderr, "DataBlock: %s\n ", keyphrase ); 180859599516SKenneth E. Jansen fprintf(stderr, "Please recheck write sequence \n"); 180959599516SKenneth E. Jansen if( Strict_Error ) { 181059599516SKenneth E. Jansen fprintf(stderr, "fatal error: cannot continue, returning out of call\n"); 181159599516SKenneth E. Jansen endTimer(&timer_end); 181259599516SKenneth E. Jansen printPerf("writedatablock", timer_start, timer_end, 0, 0, ""); 181359599516SKenneth E. Jansen return; 181459599516SKenneth E. Jansen } 181559599516SKenneth E. Jansen } 181659599516SKenneth E. Jansen 181759599516SKenneth E. Jansen FILE* fileObject = fileArray[ filePtr ] ; 181859599516SKenneth E. Jansen size_t type_size=typeSize( datatype ); 181959599516SKenneth E. Jansen isBinary( iotype ); 182059599516SKenneth E. Jansen 1821bae968b9SCameron Smith LastHeaderKey.erase(filePtr); 1822bae968b9SCameron Smith 182359599516SKenneth E. Jansen if ( header_type[filePtr] != (int)type_size ) { 182459599516SKenneth E. Jansen fprintf(stderr,"header and datablock differ on typeof data in the block for\n"); 182559599516SKenneth E. Jansen fprintf(stderr,"keyphrase : %s\n", keyphrase); 182659599516SKenneth E. Jansen if( Strict_Error ) { 182759599516SKenneth E. Jansen fprintf(stderr,"fatal error: cannot continue, returning out of call\n" ); 182859599516SKenneth E. Jansen endTimer(&timer_end); 182959599516SKenneth E. Jansen printPerf("writedatablock", timer_start, timer_end, 0, 0, ""); 183059599516SKenneth E. Jansen return; 183159599516SKenneth E. Jansen } 183259599516SKenneth E. Jansen } 183359599516SKenneth E. Jansen 183459599516SKenneth E. Jansen int nUnits = *nItems; 183559599516SKenneth E. Jansen 183659599516SKenneth E. Jansen if ( nUnits != DataSize ) { 183759599516SKenneth E. Jansen fprintf(stderr,"header and datablock differ on number of data items for\n"); 183859599516SKenneth E. Jansen fprintf(stderr,"keyphrase : %s\n", keyphrase); 183959599516SKenneth E. Jansen if( Strict_Error ) { 184059599516SKenneth E. Jansen fprintf(stderr,"fatal error: cannot continue, returning out of call\n" ); 184159599516SKenneth E. Jansen endTimer(&timer_end); 184259599516SKenneth E. Jansen printPerf("writedatablock", timer_start, timer_end, 0, 0, ""); 184359599516SKenneth E. Jansen return; 184459599516SKenneth E. Jansen } 184559599516SKenneth E. Jansen } 1846ea868eb1SCameron Smith writeDataBlock(fileObject,valueArray,*nItems,datatype,iotype); 184759599516SKenneth E. Jansen } 184859599516SKenneth E. Jansen else { // syncIO case 184959599516SKenneth E. Jansen MPI_Status write_data_status; 185059599516SKenneth E. Jansen isBinary( iotype ); 185159599516SKenneth E. Jansen int nUnits = *nItems; 185259599516SKenneth E. Jansen 185359599516SKenneth E. Jansen //MR CHANGE 185459599516SKenneth E. Jansen // if ( cscompare(datatype,"double") ) 185559599516SKenneth E. Jansen char* ts1 = StringStripper( datatype ); 185659599516SKenneth E. Jansen if ( cscompare("double",ts1) ) 185759599516SKenneth E. Jansen //MR CHANGE END 185859599516SKenneth E. Jansen { 185959599516SKenneth E. Jansen memcpy((PhastaIOActiveFiles[i]->double_chunk+DB_HEADER_SIZE/sizeof(double)), valueArray, nUnits*sizeof(double)); 186059599516SKenneth E. Jansen MPI_File_write_at_all_begin( PhastaIOActiveFiles[i]->file_handle, 186159599516SKenneth E. Jansen PhastaIOActiveFiles[i]->my_offset, 186259599516SKenneth E. Jansen PhastaIOActiveFiles[i]->double_chunk, 186359599516SKenneth E. Jansen //BLOCK_SIZE/sizeof(double), 186459599516SKenneth E. Jansen nUnits+DB_HEADER_SIZE/sizeof(double), 186559599516SKenneth E. Jansen MPI_DOUBLE ); 186659599516SKenneth E. Jansen MPI_File_write_at_all_end( PhastaIOActiveFiles[i]->file_handle, 186759599516SKenneth E. Jansen PhastaIOActiveFiles[i]->double_chunk, 186859599516SKenneth E. Jansen &write_data_status ); 186959599516SKenneth E. Jansen data_size=8*nUnits; 187059599516SKenneth E. Jansen } 187159599516SKenneth E. Jansen //MR CHANGE 187259599516SKenneth E. Jansen // else if ( cscompare ( datatype, "integer")) 187359599516SKenneth E. Jansen else if ( cscompare("integer",ts1) ) 187459599516SKenneth E. Jansen //MR CHANGE END 187559599516SKenneth E. Jansen { 187659599516SKenneth E. Jansen memcpy((PhastaIOActiveFiles[i]->int_chunk+DB_HEADER_SIZE/sizeof(int)), valueArray, nUnits*sizeof(int)); 187759599516SKenneth E. Jansen MPI_File_write_at_all_begin( PhastaIOActiveFiles[i]->file_handle, 187859599516SKenneth E. Jansen PhastaIOActiveFiles[i]->my_offset, 187959599516SKenneth E. Jansen PhastaIOActiveFiles[i]->int_chunk, 188059599516SKenneth E. Jansen nUnits+DB_HEADER_SIZE/sizeof(int), 188159599516SKenneth E. Jansen MPI_INT ); 188259599516SKenneth E. Jansen MPI_File_write_at_all_end( PhastaIOActiveFiles[i]->file_handle, 188359599516SKenneth E. Jansen PhastaIOActiveFiles[i]->int_chunk, 188459599516SKenneth E. Jansen &write_data_status ); 188559599516SKenneth E. Jansen data_size=4*nUnits; 188659599516SKenneth E. Jansen } 188759599516SKenneth E. Jansen else { 188859599516SKenneth E. Jansen printf("Error: writedatablock - DATA_TYPE_ILLEGAL - %s\n",datatype); 188959599516SKenneth E. Jansen endTimer(&timer_end); 189059599516SKenneth E. Jansen printPerf("writedatablock", timer_start, timer_end, 0, 0, ""); 189159599516SKenneth E. Jansen return; 189259599516SKenneth E. Jansen } 189359599516SKenneth E. Jansen free(ts1); 189459599516SKenneth E. Jansen } 189559599516SKenneth E. Jansen 189659599516SKenneth E. Jansen endTimer(&timer_end); 189759599516SKenneth E. Jansen char extra_msg[1024]; 189859599516SKenneth E. Jansen memset(extra_msg, '\0', 1024); 189959599516SKenneth E. Jansen char* key = StringStripper(keyphrase); 190059599516SKenneth E. Jansen sprintf(extra_msg, " field is %s ", key); 190159599516SKenneth E. Jansen printPerf("writedatablock", timer_start, timer_end, data_size, 1, extra_msg); 190259599516SKenneth E. Jansen free(key); 190359599516SKenneth E. Jansen 190459599516SKenneth E. Jansen } 190559599516SKenneth E. Jansen 1906103be424SCameron Smith void SwapArrayByteOrder( void* array, int nbytes, int nItems ) 190759599516SKenneth E. Jansen { 190859599516SKenneth E. Jansen /* This swaps the byte order for the array of nItems each 190959599516SKenneth E. Jansen of size nbytes , This will be called only locally */ 191059599516SKenneth E. Jansen int i,j; 191159599516SKenneth E. Jansen unsigned char* ucDst = (unsigned char*)array; 191259599516SKenneth E. Jansen for(i=0; i < nItems; i++) { 191359599516SKenneth E. Jansen for(j=0; j < (nbytes/2); j++) 191459599516SKenneth E. Jansen std::swap( ucDst[j] , ucDst[(nbytes - 1) - j] ); 191559599516SKenneth E. Jansen ucDst += nbytes; 191659599516SKenneth E. Jansen } 191759599516SKenneth E. Jansen } 191859599516SKenneth E. Jansen 1919103be424SCameron Smith void writestring( int* fileDescriptor, const char inString[] ) 192059599516SKenneth E. Jansen { 192159599516SKenneth E. Jansen int filePtr = *fileDescriptor - 1; 192259599516SKenneth E. Jansen FILE* fileObject = fileArray[filePtr] ; 192359599516SKenneth E. Jansen fprintf(fileObject,"%s",inString ); 192459599516SKenneth E. Jansen return; 192559599516SKenneth E. Jansen } 192659599516SKenneth E. Jansen 1927103be424SCameron Smith void Gather_Headers( int* fileDescriptor, vector< string >& headers ) 192859599516SKenneth E. Jansen { 192959599516SKenneth E. Jansen FILE* fileObject; 193059599516SKenneth E. Jansen char Line[1024]; 193159599516SKenneth E. Jansen 193259599516SKenneth E. Jansen fileObject = fileArray[ (*fileDescriptor)-1 ]; 193359599516SKenneth E. Jansen 193459599516SKenneth E. Jansen while( !feof(fileObject) ) { 193559599516SKenneth E. Jansen fgets( Line, 1024, fileObject); 193659599516SKenneth E. Jansen if ( Line[0] == '#' ) { 193759599516SKenneth E. Jansen headers.push_back( Line ); 193859599516SKenneth E. Jansen } else { 193959599516SKenneth E. Jansen break; 194059599516SKenneth E. Jansen } 194159599516SKenneth E. Jansen } 194259599516SKenneth E. Jansen rewind( fileObject ); 194359599516SKenneth E. Jansen clearerr( fileObject ); 194459599516SKenneth E. Jansen } 194559599516SKenneth E. Jansen 1946103be424SCameron Smith void isWrong( void ) { 1947103be424SCameron Smith (Wrong_Endian) ? fprintf(stdout,"YES\n") : fprintf(stdout,"NO\n"); 1948103be424SCameron Smith } 194959599516SKenneth E. Jansen 1950103be424SCameron Smith void togglestrictmode( void ) { Strict_Error = !Strict_Error; } 1951103be424SCameron Smith 1952103be424SCameron Smith int isLittleEndian( void ) 195359599516SKenneth E. Jansen { 195459599516SKenneth E. Jansen // this function returns a 1 if the current running architecture is 195559599516SKenneth E. Jansen // LittleEndian Byte Ordered, else it returns a zero 195659599516SKenneth E. Jansen union { 195759599516SKenneth E. Jansen long a; 195859599516SKenneth E. Jansen char c[sizeof( long )]; 195959599516SKenneth E. Jansen } endianUnion; 196059599516SKenneth E. Jansen endianUnion.a = 1 ; 196159599516SKenneth E. Jansen if ( endianUnion.c[sizeof(long)-1] != 1 ) return 1 ; 196259599516SKenneth E. Jansen else return 0; 196359599516SKenneth E. Jansen } 196459599516SKenneth E. Jansen 196559599516SKenneth E. Jansen namespace PHASTA { 196659599516SKenneth E. Jansen const char* const PhastaIO_traits<int>::type_string = "integer"; 196759599516SKenneth E. Jansen const char* const PhastaIO_traits<double>::type_string = "double"; 196859599516SKenneth E. Jansen } 1969