1 //===- NeonEmitter.h - Generate arm_neon.h for use with clang ---*- C++ -*-===//
3 // The LLVM Compiler Infrastructure
5 // This file is distributed under the University of Illinois Open Source
6 // License. See LICENSE.TXT for details.
8 //===----------------------------------------------------------------------===//
10 // This tablegen backend is responsible for emitting arm_neon.h, which includes
11 // a declaration and definition of each function specified by the ARM NEON
12 // compiler interface. See ARM document DUI0348B.
14 //===----------------------------------------------------------------------===//
16 #ifndef NEON_EMITTER_H
17 #define NEON_EMITTER_H
20 #include "TableGenBackend.h"
21 #include "llvm/ADT/DenseMap.h"
22 #include "llvm/ADT/StringMap.h"
77 ClassI, // generic integer instruction, e.g., "i8" suffix
78 ClassS, // signed/unsigned/poly, e.g., "s8", "u8" or "p8" suffix
79 ClassW, // width-specific instruction, e.g., "8" suffix
80 ClassB // bitcast arguments with enum argument to specify type
85 class NeonEmitter : public TableGenBackend {
86 RecordKeeper &Records;
87 StringMap<OpKind> OpMap;
88 DenseMap<Record*, ClassKind> ClassMap;
91 NeonEmitter(RecordKeeper &R) : Records(R) {
92 OpMap["OP_NONE"] = OpNone;
93 OpMap["OP_ADD"] = OpAdd;
94 OpMap["OP_ADDL"] = OpAddl;
95 OpMap["OP_ADDW"] = OpAddw;
96 OpMap["OP_SUB"] = OpSub;
97 OpMap["OP_SUBL"] = OpSubl;
98 OpMap["OP_SUBW"] = OpSubw;
99 OpMap["OP_MUL"] = OpMul;
100 OpMap["OP_MULL"] = OpMull;
101 OpMap["OP_MLA"] = OpMla;
102 OpMap["OP_MLAL"] = OpMlal;
103 OpMap["OP_MLS"] = OpMls;
104 OpMap["OP_MLSL"] = OpMlsl;
105 OpMap["OP_MUL_N"] = OpMulN;
106 OpMap["OP_MULL_N"]= OpMullN;
107 OpMap["OP_MLA_N"] = OpMlaN;
108 OpMap["OP_MLS_N"] = OpMlsN;
109 OpMap["OP_MLAL_N"] = OpMlalN;
110 OpMap["OP_MLSL_N"] = OpMlslN;
111 OpMap["OP_MUL_LN"]= OpMulLane;
112 OpMap["OP_MULL_LN"] = OpMullLane;
113 OpMap["OP_MLA_LN"]= OpMlaLane;
114 OpMap["OP_MLS_LN"]= OpMlsLane;
115 OpMap["OP_MLAL_LN"] = OpMlalLane;
116 OpMap["OP_MLSL_LN"] = OpMlslLane;
117 OpMap["OP_EQ"] = OpEq;
118 OpMap["OP_GE"] = OpGe;
119 OpMap["OP_LE"] = OpLe;
120 OpMap["OP_GT"] = OpGt;
121 OpMap["OP_LT"] = OpLt;
122 OpMap["OP_NEG"] = OpNeg;
123 OpMap["OP_NOT"] = OpNot;
124 OpMap["OP_AND"] = OpAnd;
125 OpMap["OP_OR"] = OpOr;
126 OpMap["OP_XOR"] = OpXor;
127 OpMap["OP_ANDN"] = OpAndNot;
128 OpMap["OP_ORN"] = OpOrNot;
129 OpMap["OP_CAST"] = OpCast;
130 OpMap["OP_CONC"] = OpConcat;
131 OpMap["OP_HI"] = OpHi;
132 OpMap["OP_LO"] = OpLo;
133 OpMap["OP_DUP"] = OpDup;
134 OpMap["OP_DUP_LN"] = OpDupLane;
135 OpMap["OP_SEL"] = OpSelect;
136 OpMap["OP_REV16"] = OpRev16;
137 OpMap["OP_REV32"] = OpRev32;
138 OpMap["OP_REV64"] = OpRev64;
139 OpMap["OP_REINT"] = OpReinterpret;
141 Record *SI = R.getClass("SInst");
142 Record *II = R.getClass("IInst");
143 Record *WI = R.getClass("WInst");
144 ClassMap[SI] = ClassS;
145 ClassMap[II] = ClassI;
146 ClassMap[WI] = ClassW;
149 // run - Emit arm_neon.h.inc
150 void run(raw_ostream &o);
152 // runHeader - Emit all the __builtin prototypes used in arm_neon.h
153 void runHeader(raw_ostream &o);
156 void emitIntrinsic(raw_ostream &OS, Record *R);
159 } // End llvm namespace