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"
85 ClassI, // generic integer instruction, e.g., "i8" suffix
86 ClassS, // signed/unsigned/poly, e.g., "s8", "u8" or "p8" suffix
87 ClassW, // width-specific instruction, e.g., "8" suffix
88 ClassB // bitcast arguments with enum argument to specify type
93 class NeonEmitter : public TableGenBackend {
94 RecordKeeper &Records;
95 StringMap<OpKind> OpMap;
96 DenseMap<Record*, ClassKind> ClassMap;
99 NeonEmitter(RecordKeeper &R) : Records(R) {
100 OpMap["OP_NONE"] = OpNone;
101 OpMap["OP_ADD"] = OpAdd;
102 OpMap["OP_ADDL"] = OpAddl;
103 OpMap["OP_ADDW"] = OpAddw;
104 OpMap["OP_SUB"] = OpSub;
105 OpMap["OP_SUBL"] = OpSubl;
106 OpMap["OP_SUBW"] = OpSubw;
107 OpMap["OP_MUL"] = OpMul;
108 OpMap["OP_MULL"] = OpMull;
109 OpMap["OP_MLA"] = OpMla;
110 OpMap["OP_MLAL"] = OpMlal;
111 OpMap["OP_MLS"] = OpMls;
112 OpMap["OP_MLSL"] = OpMlsl;
113 OpMap["OP_MUL_N"] = OpMulN;
114 OpMap["OP_MULL_N"]= OpMullN;
115 OpMap["OP_MLA_N"] = OpMlaN;
116 OpMap["OP_MLS_N"] = OpMlsN;
117 OpMap["OP_MLAL_N"] = OpMlalN;
118 OpMap["OP_MLSL_N"] = OpMlslN;
119 OpMap["OP_MUL_LN"]= OpMulLane;
120 OpMap["OP_MULL_LN"] = OpMullLane;
121 OpMap["OP_MLA_LN"]= OpMlaLane;
122 OpMap["OP_MLS_LN"]= OpMlsLane;
123 OpMap["OP_MLAL_LN"] = OpMlalLane;
124 OpMap["OP_MLSL_LN"] = OpMlslLane;
125 OpMap["OP_QDMULL_LN"] = OpQDMullLane;
126 OpMap["OP_QDMLAL_LN"] = OpQDMlalLane;
127 OpMap["OP_QDMLSL_LN"] = OpQDMlslLane;
128 OpMap["OP_QDMULH_LN"] = OpQDMulhLane;
129 OpMap["OP_QRDMULH_LN"] = OpQRDMulhLane;
130 OpMap["OP_EQ"] = OpEq;
131 OpMap["OP_GE"] = OpGe;
132 OpMap["OP_LE"] = OpLe;
133 OpMap["OP_GT"] = OpGt;
134 OpMap["OP_LT"] = OpLt;
135 OpMap["OP_NEG"] = OpNeg;
136 OpMap["OP_NOT"] = OpNot;
137 OpMap["OP_AND"] = OpAnd;
138 OpMap["OP_OR"] = OpOr;
139 OpMap["OP_XOR"] = OpXor;
140 OpMap["OP_ANDN"] = OpAndNot;
141 OpMap["OP_ORN"] = OpOrNot;
142 OpMap["OP_CAST"] = OpCast;
143 OpMap["OP_CONC"] = OpConcat;
144 OpMap["OP_HI"] = OpHi;
145 OpMap["OP_LO"] = OpLo;
146 OpMap["OP_DUP"] = OpDup;
147 OpMap["OP_DUP_LN"] = OpDupLane;
148 OpMap["OP_SEL"] = OpSelect;
149 OpMap["OP_REV16"] = OpRev16;
150 OpMap["OP_REV32"] = OpRev32;
151 OpMap["OP_REV64"] = OpRev64;
152 OpMap["OP_REINT"] = OpReinterpret;
153 OpMap["OP_ABDL"] = OpAbdl;
154 OpMap["OP_ABA"] = OpAba;
155 OpMap["OP_ABAL"] = OpAbal;
157 Record *SI = R.getClass("SInst");
158 Record *II = R.getClass("IInst");
159 Record *WI = R.getClass("WInst");
160 ClassMap[SI] = ClassS;
161 ClassMap[II] = ClassI;
162 ClassMap[WI] = ClassW;
165 // run - Emit arm_neon.h.inc
166 void run(raw_ostream &o);
168 // runHeader - Emit all the __builtin prototypes used in arm_neon.h
169 void runHeader(raw_ostream &o);
171 // runTests - Emit tests for all the Neon intrinsics.
172 void runTests(raw_ostream &o);
175 void emitIntrinsic(raw_ostream &OS, Record *R);
178 } // End llvm namespace