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
|
#include <kel/lbm/lbm.hpp>
#include <AdaptiveCpp/sycl/sycl.hpp>
namespace kel {
namespace lbm {
namespace sch {
using namespace saw::schema;
template<typename T, typename Desc>
using CellStruct = Struct<
Member<FixedArray<T,Desc::Q>, "dfs">,
Member<FixedArray<T,Desc::Q>, "dfs_old">,
Member<UInt8, "info">,
Member<Vector<T,Desc::D>, "velocity">,
Member<Vector<T,Desc::D>, "force">
>;
}
template<typename T, typename Desc>
saw::error_or<void> step(){
return saw::make_void();
}
}
}
template<typename T, typename Desc>
saw::error_or<void> kel_main(int argc, char** argv){
using namespace kel;
using dfi = lbm::df_info<T,Desc>;
auto eo_lbm_dir = lbm::output_directory();
if(eo_lbm_dir.is_error()){
return std::move(eo_lbm_dir.get_error());
}
auto& lbm_dir = eo_lbm_dir.get_value();
auto out_dir = lbm_dir / "poiseulle_particles_2d_gpu";
lbm::converter<lbm::sch::Float64> conv {
// delta_x
{{1.0}},
// delta_t
{{1.0}}
};
uint64_t x_d = 256u;
uint64_t y_d = 64u;
saw::data<sch::FixedArray<sch::UInt64,Desc::D>> meta{{x_d,y_d}};
saw::data<sch::Array<lbm::sch::CellStruct<T,Desc>,Desc::D>> lbm_data{meta};
acpp::sycl::queue sycl_q;
sycl_q.wait();
{
auto eov = setup_initial_conditions(lbm_data);
if(eov.is_error()){
return eov;
}
}
return saw::make_void();
}
using FloatT = kel::sch::Float32;
int main(int argc, char** argv){
auto eov = kel_main<FloatT,kel::lbm::sch::D2Q9>(argc, argv);
if(eov.is_error()){
auto& err = eov.get_error();
std::cerr<<"[Error] "<<err.get_category();
auto err_msg = err.get_message();
if(err_msg.size() > 0u){
std::cerr<<" - "<<err_msg;
}
std::cerr<<std::endl;
return err.get_id();
}
return 0;
}
|
