/* * JGL@SAFARI */ /** * CPU code with Thrust */ #include #include #include #include #include #include #include #include #include #include #include #include #include #include #include #include #include #include #include #include #include #include #include "../../support/common.h" #include "../../support/timer.h" #define XSTR(x) STR(x) #define STR(x) #x #define ANSI_COLOR_RED "\x1b[31m" #define ANSI_COLOR_GREEN "\x1b[32m" #define ANSI_COLOR_RESET "\x1b[0m" // Pointer declaration static T* A; static T* C; static T* C2; /** * @brief creates input arrays * @param nr_elements how many elements in input arrays */ static void read_input(T* A, unsigned int nr_elements) { //srand(0); printf("nr_elements\t%u\t", nr_elements); for (unsigned int i = 0; i < nr_elements; i++) { //A[i] = (T) (rand()) % 2; A[i] = i; } } /** * @brief compute output in the host */ static T reduction_host(T* A, unsigned int nr_elements) { T count = 0; for (unsigned int i = 0; i < nr_elements; i++) { count += A[i]; } return count; } // Params --------------------------------------------------------------------- typedef struct Params { unsigned int input_size; int n_warmup; int n_reps; int exp; int n_threads; }Params; void usage() { fprintf(stderr, "\nUsage: ./program [options]" "\n" "\nGeneral options:" "\n -h help" "\n -w # of untimed warmup iterations (default=1)" "\n -e # of timed repetition iterations (default=3)" "\n -x Weak (0) or strong (1) scaling (default=0)" "\n -t # of threads (default=8)" "\n" "\nBenchmark-specific options:" "\n -i input size (default=2M elements)" "\n"); } struct Params input_params(int argc, char **argv) { struct Params p; p.input_size = 2 << 20; p.n_warmup = 1; p.n_reps = 3; p.exp = 0; p.n_threads = 1; int opt; while((opt = getopt(argc, argv, "hi:w:e:x:t:")) >= 0) { switch(opt) { case 'h': usage(); exit(0); break; case 'i': p.input_size = atoi(optarg); break; case 'w': p.n_warmup = atoi(optarg); break; case 'e': p.n_reps = atoi(optarg); break; case 'x': p.exp = atoi(optarg); break; case 't': p.n_threads = atoi(optarg); break; default: fprintf(stderr, "\nUnrecognized option!\n"); usage(); exit(0); } } assert(p.n_threads > 0 && "Invalid # of threads!"); return p; } /** * @brief Main of the Host Application. */ int main(int argc, char **argv) { struct Params p = input_params(argc, argv); unsigned int nr_of_dpus = 1; unsigned int i = 0; const unsigned int input_size = p.exp == 0 ? p.input_size * p.n_threads : p.input_size; assert(input_size % (p.n_threads) == 0 && "Input size!"); // Input/output allocation A = (T*)malloc(input_size * sizeof(T)); C = (T*)malloc(input_size * sizeof(T)); C2 = (T*)malloc(input_size * sizeof(T)); T *bufferA = A; T *bufferC = C2; T count = 0; T count_host = 0; // Create an input file with arbitrary data. read_input(A, input_size); // Timer declaration Timer timer; float time_gpu = 0; thrust::omp::vector h_output(input_size); // Loop over main kernel for(int rep = 0; rep < p.n_warmup + p.n_reps; rep++) { // Compute output on CPU (performance comparison and verification purposes) if(rep >= p.n_warmup) start(&timer, 0, 0); count_host = reduction_host(A, input_size); if(rep >= p.n_warmup) stop(&timer, 0); thrust::omp::vector d_input(input_size); memcpy(thrust::raw_pointer_cast(&d_input[0]), A, input_size * sizeof(T)); omp_set_num_threads(p.n_threads); unsigned int nr_threads = 0; #pragma omp parallel #pragma omp atomic nr_threads++; if(rep >= p.n_warmup) start(&timer, 1, 0); count = thrust::reduce(thrust::omp::par, d_input.begin(), d_input.end()); if(rep >= p.n_warmup) stop(&timer, 1); h_output = d_input; // Check output bool status = true; if(count_host != count){ status = false; printf("%lu -- %lu\n", count, count_host); } if (status) { printf("[" ANSI_COLOR_GREEN "OK" ANSI_COLOR_RESET "] Outputs are equal\n"); if(rep >= p.n_warmup) { printf("[::] RED CPU | n_threads=%d e_type=%s n_elements=%u " "| throughput_seq_MBps=%f throughput_MBps=%f", nr_threads, XSTR(T), input_size, input_size * sizeof(T) / timer.time[0], input_size * sizeof(T) / timer.time[1]); printf(" throughput_seq_MOpps=%f throughput_MOpps=%f", input_size / timer.time[0], input_size / timer.time[1]); printall(&timer, 1); } } else { printf("[" ANSI_COLOR_RED "ERROR" ANSI_COLOR_RESET "] Outputs differ!\n"); } } // Print timing results //printf("CPU "); //print(&timer, 0, p.n_reps); //printf("Kernel "); //print(&timer, 1, p.n_reps); // Deallocation free(A); free(C); free(C2); return 0; }