denshooter/genode
1
0
Fork 0
mirror of https://github.com/mmueller41/genode.git synced 2026-01-21 20:42:56 +01:00
Code Issues Packages Projects Releases Wiki Activity

Merge branch 'gpgpu' of https://github.com/mmueller41/genode into gpgpu

Browse Source 
Adding print_vgpu_bench method for printing bench data from vgpu
ô
This commit is contained in:
amarmemic
2022-11-10 10:49:02 +01:00
parent 6859f714b2 87000c2cf0
commit c40ae200bd
5 changed files with 6 additions and 6 deletions
Download Patch File Download Diff File Expand all files Collapse all files

2
repos/dde_uos-intel-gpgpu/src/uos-intel-gpgpu

Submodule repos/dde_uos-intel-gpgpu/src/uos-intel-gpgpu updated: 113e28173f...06c1b3f205

4
repos/hello_gpgpu/src/hello_gpgpu/CL/cl.cc
View File

@@ -622,7 +622,7 @@ clCreateProgramWithBinary(cl_context context,
return NULL;
}
cl_program p = (cl_program)g_cl_genode->alloc(sizeof(_cl_program));
cl_program p = (cl_program)g_cl_genode->alloc(sizeof(struct _cl_program));
p->binary = (uint8_t*)binaries[0];
p->size = lengths[0];
@@ -1428,7 +1428,7 @@ clEnqueueNDRangeKernel(cl_command_queue command_queue,
}
// create copy of kernel (vm and driver should not modify the same kernel)
kernel_config* kcopy = new(g_cl_genode->getAlloc()) kernel_config();
struct kernel_config* kcopy = new(g_cl_genode->getAlloc()) kernel_config();
*kcopy = *kc;
// also copy buff configs

1
repos/hello_gpgpu/src/hello_gpgpu/benchmark/doitgen/doitgen.cl
View File

@@ -30,7 +30,6 @@ __kernel void doitgen_kernel1(int nr, int nq, int np, __global DATA_TYPE *A, __g
for (int s = 0; s < np; s++)
{
sum[r * (nq * np) + q * np + p] = sum[r * (nq * np) + q * np + p] + A[r * (nq * np) + q * np + s] * C4[s * np + p];
//sum[r * (nq * np) + q * np + p] = (float)q;
}
}
}

4
repos/hello_gpgpu/src/hello_gpgpu/main.cc
View File

@@ -50,7 +50,7 @@ void testvm_construct(Genode::Env &env)
Genode::log("===Run bicg===");
ns_bicg::main(0, 0);
Genode::log("===Run doitgen===");
ns_doitgen::main(0, 0); // Number of misses: 2080768 + GPU kernel1 takes very long
ns_doitgen::main(0, 0);
Genode::log("===Run gemm===");
ns_gemm::main(0, 0);
Genode::log("===Run gemver===");
@@ -70,7 +70,7 @@ void testvm_construct(Genode::Env &env)
ns_lu::main(0, 0); // Non-Matching CPU-GPU Outputs Beyond Error Threshold of 0.05 Percent: 516
Genode::log("===Run correlation===");
ns_correlation::main(0, 0); // Non-Matching CPU-GPU Outputs Beyond Error Threshold of 1.05 Percent: 1
ns_correlation::main(0, 0);
Genode::log("===Run covariance===");
ns_covariance::main(0, 0);

1
repos/hello_gpgpu/src/hello_gpgpu/polybench.cc
View File

@@ -30,6 +30,7 @@
#endif
#define POLYBENCH_TIME 1
#define POLYBENCH_CYCLE_ACCURATE_TIMER
int polybench_papi_counters_threadid = POLYBENCH_THREAD_MONITOR;
double polybench_program_total_flops = 0;