Нахождение максимального значения элемента И его положения с помощью CUDA Thrust

Как мне получить не только значение, но и положение максимального (минимального) элемента ( res.val и res.pos )?

thrust::host_vector<float> h_vec(100);
thrust::generate(h_vec.begin(), h_vec.end(), rand);
thrust::device_vector<float> d_vec = h_vec;

T res = -1;
res = thrust::reduce(d_vec.begin(), d_vec.end(), res, thrust::maximum<T>());