1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
67
68
69
70
71
72
73
74
75
76
77
78
79
80
81
82
83
84
85
86
87
88
89
90
91
92
93
94
95
96
97
98
99
|
/// \file CudaManager.cu
/// \author Johannes de Fine Licht (johannes.definelicht@cern.ch)
#include "VecGeom/management/CudaManager.h"
#include <stdio.h>
#include "VecGeom/backend/cuda/Backend.h"
namespace vecgeom {
inline namespace cuda {
__global__ void InitDeviceCompactPlacedVolBufferPtrCudaKernel(void *gpu_ptr)
{
// gpu_ptr is some pointer on the device that was allocated by some other means
globaldevicegeomdata::gCompactPlacedVolBuffer = (vecgeom::cuda::VPlacedVolume *)gpu_ptr;
}
void InitDeviceCompactPlacedVolBufferPtr(void *gpu_ptr)
{
InitDeviceCompactPlacedVolBufferPtrCudaKernel<<<1, 1>>>(gpu_ptr);
vecgeom::cxx::CudaAssertError();
}
__global__ void InitDeviceNavIndexPtrCudaKernel(void *gpu_ptr, int maxdepth)
{
// gpu_ptr is some pointer on the device that was allocated by some other means
globaldevicegeomdata::gNavIndex = (NavIndex_t *)gpu_ptr;
globaldevicegeomdata::gMaxDepth = maxdepth;
}
void InitDeviceNavIndexPtr(void *gpu_ptr, int maxdepth)
{
InitDeviceNavIndexPtrCudaKernel<<<1, 1>>>(gpu_ptr, maxdepth);
}
__global__ void CudaManagerPrintGeometryKernel(vecgeom::cuda::VPlacedVolume const *const world)
{
printf("Geometry loaded on GPU:\n");
world->PrintContent();
}
void CudaManagerPrintGeometry(vecgeom::cuda::VPlacedVolume const *const world)
{
CudaManagerPrintGeometryKernel<<<1, 1>>>(world);
cxx::CudaAssertError();
cudaDeviceSynchronize();
}
}
} // End namespace vecgeom
#ifdef VECCORE_CUDA_SINGLE_OBJ // Cuda single compilation
#include "source/Vector.cpp"
#include "source/SOA3D.cpp"
#include "source/Transformation3D.cpp"
#include "source/LogicalVolume.cpp"
#include "source/PlacedVolume.cpp"
#include "source/UnplacedVolume.cpp"
#include "source/PlacedBox.cpp"
#include "source/UnplacedBox.cpp"
#include "source/SpecializedBox.cpp"
#include "source/PlacedCone.cpp"
#include "source/UnplacedCone.cpp"
#include "source/PlacedTube.cpp"
#include "source/UnplacedTube.cpp"
#include "source/PlacedTorus.cpp"
#include "source/UnplacedTorus.cpp"
#include "source/PlacedTrd.cpp"
#include "source/UnplacedTrd.cpp"
#include "source/PlacedParallelepiped.cpp"
#include "source/UnplacedParallelepiped.cpp"
#include "source/PlacedParaboloid.cpp"
#include "source/UnplacedParaboloid.cpp"
#include "source/PlacedTrapezoid.cpp"
#include "source/UnplacedTrapezoid.cpp"
#include "source/NavigationState.cpp"
#include "source/SimpleNavigator.cpp"
#include "source/UnplacedOrb.cpp"
#include "source/PlacedOrb.cpp"
#include "source/UnplacedSphere.cpp"
#include "source/PlacedSphere.cpp"
#include "source/UnplacedBooleanVolume.cpp"
#include "source/PlacedBooleanVolume.cpp"
#endif
|
