target.cpp 1.58 KB
Newer Older
Paul's avatar
Paul committed
1
2
#include <migraph/gpu/target.hpp>
#include <migraph/gpu/lowering.hpp>
mei-ye's avatar
staging  
mei-ye committed
3
#include <migraph/memory_coloring.hpp>
Paul's avatar
Paul committed
4
5
#include <migraph/gpu/write_literals.hpp>
#include <migraph/gpu/context.hpp>
6
#include <migraph/gpu/eliminate_workspace.hpp>
7
#include <migraph/gpu/eliminate_allocation.hpp>
Paul's avatar
Paul committed
8
#include <migraph/gpu/fuse_ops.hpp>
Paul's avatar
Paul committed
9
#include <migraph/check_context.hpp>
Paul's avatar
Paul committed
10
#include <migraph/auto_contiguous.hpp>
Paul's avatar
Paul committed
11
12
#include <migraph/dead_code_elimination.hpp>
#include <migraph/simplify_reshapes.hpp>
13
#include <migraph/eliminate_contiguous.hpp>
14
#include <migraph/fwd_conv_batchnorm_rewrite.hpp>
Paul's avatar
Paul committed
15
16

namespace migraph {
Paul's avatar
Paul committed
17
namespace gpu {
Paul's avatar
Paul committed
18

Paul's avatar
Paul committed
19
std::vector<pass> target::get_passes(migraph::context& gctx) const
Paul's avatar
Paul committed
20
{
Paul's avatar
Paul committed
21
    auto& ctx = any_cast<context>(gctx);
Paul's avatar
Paul committed
22
23
24
    // clang-format off
    return
    {
Paul's avatar
Paul committed
25
26
        dead_code_elimination{},
        fwd_conv_batchnorm_rewrite{},
Paul's avatar
Paul committed
27
        dead_code_elimination{},
Paul's avatar
Paul committed
28
        auto_contiguous{},
Paul's avatar
Paul committed
29
        simplify_reshapes{},
Paul's avatar
Paul committed
30
        dead_code_elimination{},
Paul's avatar
Paul committed
31
        lowering{ctx},
mei-ye's avatar
mei-ye committed
32
        memory_coloring{},
Paul's avatar
Paul committed
33
34
        fuse_ops{},
        dead_code_elimination{},
mei-ye's avatar
mei-ye committed
35
36
            //            eliminate_workspace{},

37
        eliminate_contiguous{},
Paul's avatar
Paul committed
38
        dead_code_elimination{},
mei-ye's avatar
mei-ye committed
39

Paul's avatar
Paul committed
40
        write_literals{&ctx},
mei-ye's avatar
mei-ye committed
41
            //        eliminate_allocation{},
42
43
        check_context<context>{},
        dead_code_elimination{}
Paul's avatar
Paul committed
44
45
    };
    // clang-format on
Paul's avatar
Paul committed
46
}
Paul's avatar
Paul committed
47

Paul's avatar
Paul committed
48
std::string target::name() const { return "miopen"; }
Paul's avatar
Paul committed
49

Paul's avatar
Paul committed
50
migraph::context target::get_context() const
Paul's avatar
Paul committed
51
{
Paul's avatar
Paul committed
52
    return context{share(make_obj<miopen_handle>(&miopenCreate)),
Paul's avatar
Paul committed
53
                   share(create_rocblas_handle_ptr())};
Paul's avatar
Paul committed
54
55
}

Paul's avatar
Paul committed
56
} // namespace gpu
Paul's avatar
Paul committed
57

Paul's avatar
Paul committed
58
} // namespace migraph