@@ -23,22 +23,24 @@ namespace traccc::cuda {
2323namespace kernels {
2424// / CUDA kernel for running @c traccc::device::estimate_track_params
2525__global__ void estimate_track_params (
26+ const track_params_estimation_config config,
2627 measurement_collection_types::const_view measurements_view,
2728 edm::spacepoint_collection::const_view spacepoints_view,
2829 edm::seed_collection::const_view seed_view, const vector3 bfield,
29- const std::array<traccc::scalar, traccc::e_bound_size> stddev,
3030 bound_track_parameters_collection_types::view params_view) {
3131
32- device::estimate_track_params (details::global_index1 (), measurements_view ,
33- spacepoints_view, seed_view, bfield, stddev ,
34- params_view);
32+ device::estimate_track_params (details::global_index1 (), config ,
33+ measurements_view, spacepoints_view ,
34+ seed_view, bfield, params_view);
3535}
3636} // namespace kernels
3737
3838track_params_estimation::track_params_estimation (
39+ const track_params_estimation_config& config,
3940 const traccc::memory_resource& mr, vecmem::copy& copy, stream& str,
4041 std::unique_ptr<const Logger> logger)
4142 : messaging(std::move(logger)),
43+ m_config (config),
4244 m_mr(mr),
4345 m_copy(copy),
4446 m_stream(str),
@@ -47,8 +49,8 @@ track_params_estimation::track_params_estimation(
4749track_params_estimation::output_type track_params_estimation::operator ()(
4850 const measurement_collection_types::const_view& measurements_view,
4951 const edm::spacepoint_collection::const_view& spacepoints_view,
50- const edm::seed_collection::const_view& seeds_view, const vector3& bfield,
51- const std::array<traccc::scalar, traccc::e_bound_size>& stddev ) const {
52+ const edm::seed_collection::const_view& seeds_view,
53+ const vector3& bfield ) const {
5254
5355 // Get a convenience variable for the stream that we'll be using.
5456 cudaStream_t stream = details::get_stream (m_stream);
@@ -82,7 +84,7 @@ track_params_estimation::output_type track_params_estimation::operator()(
8284
8385 // run the kernel
8486 kernels::estimate_track_params<<<num_blocks, num_threads, 0 , stream>>> (
85- measurements_view, spacepoints_view, seeds_view, bfield, stddev ,
87+ m_config, measurements_view, spacepoints_view, seeds_view, bfield,
8688 params_buffer);
8789 TRACCC_CUDA_ERROR_CHECK (cudaGetLastError ());
8890
0 commit comments