blob: c97fabb91e9d9930606fb9f6c41892f69c5bd57c [file] [log] [blame]
Nate Begeman5ddb0872010-05-28 01:08:32 +00001//===- NeonEmitter.h - Generate arm_neon.h for use with clang ---*- C++ -*-===//
2//
3// The LLVM Compiler Infrastructure
4//
5// This file is distributed under the University of Illinois Open Source
6// License. See LICENSE.TXT for details.
7//
8//===----------------------------------------------------------------------===//
9//
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.
13//
14//===----------------------------------------------------------------------===//
15
16#ifndef NEON_EMITTER_H
17#define NEON_EMITTER_H
18
Nate Begeman73cef3e2010-06-04 01:26:15 +000019#include "Record.h"
Nate Begeman5ddb0872010-05-28 01:08:32 +000020#include "TableGenBackend.h"
Nate Begeman73cef3e2010-06-04 01:26:15 +000021#include "llvm/ADT/DenseMap.h"
22#include "llvm/ADT/StringMap.h"
23
24enum OpKind {
25 OpNone,
26 OpAdd,
27 OpSub,
28 OpMul,
29 OpMla,
30 OpMls,
31 OpEq,
32 OpGe,
33 OpLe,
34 OpGt,
35 OpLt,
36 OpNeg,
37 OpNot,
38 OpAnd,
39 OpOr,
40 OpXor,
41 OpAndNot,
42 OpOrNot,
Nate Begeman900f4672010-06-08 00:14:42 +000043 OpCast,
44 OpConcat,
45 OpDup
Nate Begeman73cef3e2010-06-04 01:26:15 +000046};
47
48enum ClassKind {
49 ClassNone,
50 ClassI,
51 ClassS,
52 ClassW,
53 ClassB
54};
Nate Begeman5ddb0872010-05-28 01:08:32 +000055
56namespace llvm {
57
58 class NeonEmitter : public TableGenBackend {
59 RecordKeeper &Records;
Nate Begeman73cef3e2010-06-04 01:26:15 +000060 StringMap<OpKind> OpMap;
61 DenseMap<Record*, ClassKind> ClassMap;
62
Nate Begeman5ddb0872010-05-28 01:08:32 +000063 public:
Nate Begeman73cef3e2010-06-04 01:26:15 +000064 NeonEmitter(RecordKeeper &R) : Records(R) {
65 OpMap["OP_NONE"] = OpNone;
66 OpMap["OP_ADD"] = OpAdd;
67 OpMap["OP_SUB"] = OpSub;
68 OpMap["OP_MUL"] = OpMul;
69 OpMap["OP_MLA"] = OpMla;
70 OpMap["OP_MLS"] = OpMls;
71 OpMap["OP_EQ"] = OpEq;
72 OpMap["OP_GE"] = OpGe;
73 OpMap["OP_LE"] = OpLe;
74 OpMap["OP_GT"] = OpGt;
75 OpMap["OP_LT"] = OpLt;
76 OpMap["OP_NEG"] = OpNeg;
77 OpMap["OP_NOT"] = OpNot;
78 OpMap["OP_AND"] = OpAnd;
79 OpMap["OP_OR"] = OpOr;
80 OpMap["OP_XOR"] = OpXor;
81 OpMap["OP_ANDN"] = OpAndNot;
82 OpMap["OP_ORN"] = OpOrNot;
83 OpMap["OP_CAST"] = OpCast;
Nate Begeman900f4672010-06-08 00:14:42 +000084 OpMap["OP_CONC"] = OpConcat;
85 OpMap["OP_DUP"] = OpDup;
Nate Begeman73cef3e2010-06-04 01:26:15 +000086
87 Record *SI = R.getClass("SInst");
88 Record *II = R.getClass("IInst");
89 Record *WI = R.getClass("WInst");
90 Record *BI = R.getClass("BInst");
91 ClassMap[SI] = ClassS;
92 ClassMap[II] = ClassI;
93 ClassMap[WI] = ClassW;
94 ClassMap[BI] = ClassB;
95 }
Nate Begeman5ddb0872010-05-28 01:08:32 +000096
Nate Begemana8979a02010-06-04 00:21:41 +000097 // run - Emit arm_neon.h.inc
Nate Begeman5ddb0872010-05-28 01:08:32 +000098 void run(raw_ostream &o);
Nate Begemana8979a02010-06-04 00:21:41 +000099
100 // runHeader - Emit all the __builtin prototypes used in arm_neon.h
101 void runHeader(raw_ostream &o);
Nate Begeman5ddb0872010-05-28 01:08:32 +0000102 };
103
104} // End llvm namespace
105
106#endif