/* * StarPU * Copyright (C) INRIA 2008-2009 (see AUTHORS file) * * This program is free software; you can redistribute it and/or modify * it under the terms of the GNU Lesser General Public License as published by * the Free Software Foundation; either version 2.1 of the License, or (at * your option) any later version. * * This program is distributed in the hope that it will be useful, but * WITHOUT ANY WARRANTY; without even the implied warranty of * MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE. * * See the GNU Lesser General Public License in COPYING.LGPL for more details. */ #include "dw_mult.h" #define TAG(taskx, tasky) ((((unsigned long long)(taskx))<<32) | (unsigned long long)(tasky)) float *A, *B, *C; starpu_data_handle A_handle, B_handle, C_handle; /* * That program should compute C = A * B * * A of size (z,y) * B of size (x,z) * C of size (x,y) |---------------| z | B | |---------------| z x |----| |---------------| | | | | | | | | | A | y | C | | | | | | | | | |----| |---------------| */ void terminate(void) { fprintf(stderr, "unpartition !!\n"); starpu_unpartition_data(C_handle, 0); starpu_delete_data(C_handle); gettimeofday(&end, NULL); double timing = (double)((end.tv_sec - start.tv_sec)*1000000 + (end.tv_usec - start.tv_usec)); display_stats(timing); #ifdef CHECK_OUTPUT /* check results */ /* compute C = C - AB */ SGEMM("N", "N", ydim, xdim, zdim, -1.0f, A, ydim, B, zdim, 1.0f, C, ydim); /* make sure C = 0 */ float err; err = SASUM(xdim*ydim, C, 1); if (err < xdim*ydim*0.001) { fprintf(stderr, "Results are OK\n"); } else { fprintf(stderr, "There were errors ... err = %f\n", err); } #endif // CHECK_OUTPUT } void callback_func(void *arg) { /* do some accounting */ int id = starpu_get_worker_id(); flop_per_worker[id] += BLAS3_FLOP(conf.m, conf.n, conf.k); ls_per_worker[id] += BLAS3_LS(conf.m, conf.n, conf.k); } static void init_problem_data(void) { unsigned i,j; #ifdef USE_CUDA if (pin) { starpu_malloc_pinned_if_possible((void **)&A, zdim*ydim*sizeof(float)); starpu_malloc_pinned_if_possible((void **)&B, xdim*zdim*sizeof(float)); starpu_malloc_pinned_if_possible((void **)&C, xdim*ydim*sizeof(float)); } else #endif { #ifdef HAVE_POSIX_MEMALIGN posix_memalign((void **)&A, 4096, zdim*ydim*sizeof(float)); posix_memalign((void **)&B, 4096, xdim*zdim*sizeof(float)); posix_memalign((void **)&C, 4096, xdim*ydim*sizeof(float)); #else A = malloc(zdim*ydim*sizeof(float)); B = malloc(xdim*zdim*sizeof(float)); C = malloc(xdim*ydim*sizeof(float)); #endif } /* fill the A and B matrices */ if (norandom) { for (j=0; j < ydim; j++) { for (i=0; i < zdim; i++) { A[j+i*ydim] = (float)(i); } } for (j=0; j < zdim; j++) { for (i=0; i < xdim; i++) { B[j+i*zdim] = (float)(j); } } } else { #ifdef NORANDOM srand(2008); STARPU_ABORT(); #endif for (j=0; j < ydim; j++) { for (i=0; i < zdim; i++) { A[j+i*ydim] = (float)(drand48()); } } for (j=0; j < zdim; j++) { for (i=0; i < xdim; i++) { B[j+i*zdim] = (float)(drand48()); } } } for (j=0; j < ydim; j++) { for (i=0; i < xdim; i++) { C[j+i*ydim] = (float)(0); } } display_memory_consumption(); } static void partition_mult_data(void) { gettimeofday(&start, NULL); starpu_register_blas_data(&A_handle, 0, (uintptr_t)A, ydim, ydim, zdim, sizeof(float)); starpu_register_blas_data(&B_handle, 0, (uintptr_t)B, zdim, zdim, xdim, sizeof(float)); starpu_register_blas_data(&C_handle, 0, (uintptr_t)C, ydim, ydim, xdim, sizeof(float)); starpu_data_set_wb_mask(C_handle, 1<<0); conf.k = zdim; conf.m = ydim/nslicesy; conf.n = xdim/nslicesx; starpu_filter f; f.filter_func = starpu_vertical_block_filter_func; f.filter_arg = nslicesx; starpu_filter f2; f2.filter_func = starpu_block_filter_func; f2.filter_arg = nslicesy; starpu_partition_data(B_handle, &f); starpu_partition_data(A_handle, &f2); starpu_map_filters(C_handle, 2, &f, &f2); } static starpu_codelet cl = { .where = CORE|CUDA|GORDON, .core_func = core_mult, #ifdef USE_CUDA .cuda_func = cublas_mult, #endif #ifdef USE_GORDON #ifdef SPU_FUNC_SGEMM .gordon_func = SPU_FUNC_SGEMM, #else #warning SPU_FUNC_SGEMM is not available #endif #endif .nbuffers = 3 }; static void launch_codelets(void) { #ifdef USE_FXT fxt_register_thread(0); #endif /* partition the work into slices */ unsigned taskx, tasky; srand(time(NULL)); /* should we use a single performance model for all archs and use an * acceleration factor ? */ if (use_common_model) { cl.model = &sgemm_model_common; } else { cl.model = &sgemm_model; } for (taskx = 0; taskx < nslicesx; taskx++) { for (tasky = 0; tasky < nslicesy; tasky++) { /* A B[task] = C[task] */ struct starpu_task *task = starpu_task_create(); task->cl = &cl; task->cl_arg = &conf; task->cl_arg_size = sizeof(struct block_conf); task->callback_func = callback_func; task->callback_arg = NULL; starpu_tag_t tag = TAG(taskx, tasky); task->use_tag = 1; task->tag_id = tag; task->buffers[0].handle = get_sub_data(A_handle, 1, tasky); task->buffers[0].mode = STARPU_R; task->buffers[1].handle = get_sub_data(B_handle, 1, taskx); task->buffers[1].mode = STARPU_R; task->buffers[2].handle = get_sub_data(C_handle, 2, taskx, tasky); task->buffers[2].mode = STARPU_RW; starpu_submit_task(task); } } } int main(__attribute__ ((unused)) int argc, __attribute__ ((unused)) char **argv) { parse_args(argc, argv); /* start the runtime */ starpu_init(NULL); starpu_helper_init_cublas(); init_problem_data(); partition_mult_data(); launch_codelets(); starpu_wait_all_tasks(); terminate(); starpu_helper_shutdown_cublas(); starpu_shutdown(); return 0; }