Classes
class	DeviceExperimentCuts

class	SeedFinder

struct	DeviceSelector
	Custom device selector that refuses to select NVIDIA OpenCL backends. More...

class	QueueWrapper

Typedefs
template<typename T >
using	device_array = std::unique_ptr< T, detail::DeviceArrayDeleter >
	Convenience type for using (primitive) variable arrays on a SYCL device.

Functions
void	createSeedsForGroupSycl (QueueWrapper wrappedQueue, vecmem::memory_resource &resource, vecmem::memory_resource *device_resource, const detail::DeviceSeedFinderConfig &seedFinderConfig, const DeviceExperimentCuts &deviceCuts, vecmem::vector< detail::DeviceSpacePoint > &bottomSPs, vecmem::vector< detail::DeviceSpacePoint > &middleSPs, vecmem::vector< detail::DeviceSpacePoint > &topSPs, std::vector< std::vector< detail::SeedData >> &seeds)
	Seedfinding algorithm implemented in SYCL.

cl::sycl::nd_range< 1 >	calculate1DimNDRange (const uint32_t numThreads, const uint32_t workGroupSize)
	Calculate global range of 1 dimensional nd_range for kernel execution.

cl::sycl::nd_range< 2 >	calculate2DimNDRange (const uint32_t numThreadsDim0, const uint32_t numThreadsDim1, const uint32_t workGroupSize)
	Calculate global and local range of 2 dimensional nd_range for kernel execution.

void	listPlatforms ()
	This function allows us to list available SYCL platforms and devices.

template<typename T >
device_array< T >	make_device_array (std::size_t size, cl::sycl::queue &queue)
	Function creating a primitive array in SYCL device memory.

Typedef Documentation

template<typename T >

Convenience type for using (primitive) variable arrays on a SYCL device.

Definition at line 43 of file Arrays.hpp.

View newest version in sPHENIX GitHub at line 43 of file Arrays.hpp

Function Documentation

cl::sycl::nd_range< 1 > Acts::Sycl::calculate1DimNDRange	(	const uint32_t	numThreads,
		const uint32_t	workGroupSize
	)

Calculate global range of 1 dimensional nd_range for kernel execution.

Parameters

[in]	numThreads	is the number of threads globally
[in]	workGroupSize	is the number of threads in one work group

Calculates the global dimension of the nd_range, which is the smallest multiple of workGroupSize that is not smaller than numThreads.

Definition at line 13 of file CalculateNdRange.cpp.

View newest version in sPHENIX GitHub at line 13 of file CalculateNdRange.cpp

Here is the caller graph for this function:

cl::sycl::nd_range< 2 > Acts::Sycl::calculate2DimNDRange	(	const uint32_t	numThreadsDim0,
		const uint32_t	numThreadsDim1,
		const uint32_t	workGroupSize
	)

Calculate global and local range of 2 dimensional nd_range for kernel execution.

Parameters

[in]	numThreadsDim0	is the number of threads globally in the first dimension
[in]	numThreadsDim1	is the number of threads globally in the second dimension
[in]	workGroupSize	is the number of threads in one work group

Local range is calculated the following way:

local range dimensions multiplied together should be equal to workGroupSize
if workGroupSize > numThreadsDim1: set local range in the second dimension to be equal to the smallest factor of 2, that is not smaller that the number of threads globally in the second dimension
else: local range is {1, workGroupSize}

Global range is calculated the following way:

set the number of threads in both dimensions to the smallest multiple of the work group size in that dimension

Definition at line 20 of file CalculateNdRange.cpp.

View newest version in sPHENIX GitHub at line 20 of file CalculateNdRange.cpp

Here is the caller graph for this function:

void Acts::Sycl::createSeedsForGroupSycl	(	QueueWrapper	wrappedQueue,
		vecmem::memory_resource &	resource,
		vecmem::memory_resource *	device_resource,
		const detail::DeviceSeedFinderConfig &	seedFinderConfig,
		const DeviceExperimentCuts &	deviceCuts,
		vecmem::vector< detail::DeviceSpacePoint > &	bottomSPs,
		vecmem::vector< detail::DeviceSpacePoint > &	middleSPs,
		vecmem::vector< detail::DeviceSpacePoint > &	topSPs,
		std::vector< std::vector< detail::SeedData >> &	seeds
	)

Seedfinding algorithm implemented in SYCL.

Parameters

[in]	wrappedQueue	is a wrapper object of the SYCL queue
[in]	resource	is the host-accessible memory resource to use
[in]	device_resource	is the optional device-accessible memory resource, necessary if `resource` is not device-accessible
[in]	seedFinderConfig	includes the required configuration parameters for the algorithm
[in]	deviceCuts	is an experiment specific object with customizable seed weight altering and seed cutting member functions
[in]	bottomSPs	an array of simplified internal space point structures of bottom space points
[in]	middleSPs	an array of simplified internal space point structures of middle space points
[in]	topSPs	an array of simplified internal space point structures of top space points
[out]	seeds	holds of the generated seed indices and weight