target.cpp 2.04 KB
Newer Older
Paul's avatar
Paul committed
1
2
#include <migraph/gpu/target.hpp>
#include <migraph/gpu/lowering.hpp>
mei-ye's avatar
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>
Paul's avatar
Paul committed
7
#include <migraph/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>
Paul's avatar
Paul committed
13
14
#include <migraph/simplify_algebra.hpp>
#include <migraph/constant_propagate.hpp>
15
#include <migraph/eliminate_contiguous.hpp>
Paul's avatar
Paul committed
16
#include <migraph/common_subexpression_elimination.hpp>
17
#include <migraph/fwd_conv_batchnorm_rewrite.hpp>
wsttiger's avatar
wsttiger committed
18
19
#include <migraph/eliminate_concat.hpp>
#include <migraph/gpu/concat_gpu_opt.hpp>
Paul's avatar
Paul committed
20
21

namespace migraph {
22
inline namespace MIGRAPH_INLINE_NS {
Paul's avatar
Paul committed
23
namespace gpu {
mei-ye's avatar
mei-ye committed
24

Paul's avatar
Paul committed
25
std::vector<pass> target::get_passes(migraph::context& gctx) const
Paul's avatar
Paul committed
26
{
Paul's avatar
Paul committed
27
    auto& ctx = any_cast<context>(gctx);
Paul's avatar
Paul committed
28
29
30
    // clang-format off
    return
    {
Paul's avatar
Paul committed
31
32
        dead_code_elimination{},
        fwd_conv_batchnorm_rewrite{},
Paul's avatar
Paul committed
33
        dead_code_elimination{},
Paul's avatar
Paul committed
34
35
        common_subexpression_elimination{},
        dead_code_elimination{},
Paul's avatar
Paul committed
36
37
38
39
        simplify_algebra{},
        dead_code_elimination{},
        constant_propagate{},
        dead_code_elimination{},
Paul's avatar
Paul committed
40
        auto_contiguous{},
Paul's avatar
Paul committed
41
        simplify_reshapes{},
Paul's avatar
Paul committed
42
        dead_code_elimination{},
Paul's avatar
Paul committed
43
        lowering{ctx},
wsttiger's avatar
wsttiger committed
44
45
        eliminate_concat{concat_gpu_optimization{}},
        dead_code_elimination{},
46
        eliminate_contiguous{},
Paul's avatar
Paul committed
47
        dead_code_elimination{},
Paul's avatar
Paul committed
48
49
        fuse_ops{&ctx},
        dead_code_elimination{},
Paul's avatar
Paul committed
50
        write_literals{&ctx},
Paul's avatar
Paul committed
51
        memory_coloring{"hip::allocate"},
Paul's avatar
Paul committed
52
53
        eliminate_workspace{},
        eliminate_allocation{"hip::allocate"},
54
55
        check_context<context>{},
        dead_code_elimination{}
Paul's avatar
Paul committed
56
57
    };
    // clang-format on
Paul's avatar
Paul committed
58
}
Paul's avatar
Paul committed
59

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

Paul's avatar
Paul committed
62
migraph::context target::get_context() const { return context{}; }
Paul's avatar
Paul committed
63
} // namespace gpu
64
} // namespace MIGRAPH_INLINE_NS
Paul's avatar
Paul committed
65
} // namespace migraph