thrust::copy between host & device is not interoperable with thrust::cuda::par.on(stream)

[jaredhoberock]

The program crashes:

#include <thrust/host_vector.h>
#include <thrust/device_vector.h>
#include <thrust/copy.h>
#include <thrust/execution_policy.h>

int main()
{           
  int N = 5000;

  cudaStream_t stream;
  cudaStreamCreate(&stream);
  thrust::host_vector<float> filterVecHost(N);      
  thrust::device_vector<float> filterVecGpu(N);     
  thrust::copy(thrust::cuda::par.on(stream), filterVecHost.begin(), filterVecHost.end(), filterVecGpu.begin()); 


  return 0;
}

Originally reported here: https://groups.google.com/d/msg/thrust-users/5q9YBPjjMrI/R5NCrB2wH6EJ

[jaredhoberock]

It might be possible to avoid this problem if we forego the execution policy-based dispatching trivial_copy_n and the like use and use cudaMemcpyDefault instead.