utils/TableGen/NeonEmitter.h

   1 //===- 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
  19 #include "Record.h"
  20 #include "TableGenBackend.h"
  21 #include "llvm/ADT/DenseMap.h"
  22 #include "llvm/ADT/StringMap.h"
  23
  24 enum OpKind {
  25   OpNone,
  26   OpAdd,
  27   OpSub,
  28   OpMul,
  29   OpMull,
  30   OpMla,
  31   OpMls,
  32   OpMulN,
  33   OpMullN,
  34   OpMlaN,
  35   OpMlsN,
  36   OpMulLane,
  37   OpMullLane,
  38   OpMlaLane,
  39   OpMlsLane,
  40   OpEq,
  41   OpGe,
  42   OpLe,
  43   OpGt,
  44   OpLt,
  45   OpNeg,
  46   OpNot,
  47   OpAnd,
  48   OpOr,
  49   OpXor,
  50   OpAndNot,
  51   OpOrNot,
  52   OpCast,
  53   OpConcat,
  54   OpDup,
  55   OpDupLane,
  56   OpHi,
  57   OpLo,
  58   OpSelect,
  59   OpRev16,
  60   OpRev32,
  61   OpRev64,
  62   OpReinterpret
  63 };
  64
  65 enum ClassKind {
  66   ClassNone,
  67   ClassI,           // generic integer instruction, e.g., "i8" suffix
  68   ClassS,           // signed/unsigned/poly, e.g., "s8", "u8" or "p8" suffix
  69   ClassW,           // width-specific instruction, e.g., "8" suffix
  70   ClassB            // bitcast arguments with enum argument to specify type
  71 };
  72
  73 namespace llvm {
  74
  75   class NeonEmitter : public TableGenBackend {
  76     RecordKeeper &Records;
  77     StringMap<OpKind> OpMap;
  78     DenseMap<Record*, ClassKind> ClassMap;
  79
  80   public:
  81     NeonEmitter(RecordKeeper &R) : Records(R) {
  82       OpMap["OP_NONE"]  = OpNone;
  83       OpMap["OP_ADD"]   = OpAdd;
  84       OpMap["OP_SUB"]   = OpSub;
  85       OpMap["OP_MUL"]   = OpMul;
  86       OpMap["OP_MULL"]  = OpMull;
  87       OpMap["OP_MLA"]   = OpMla;
  88       OpMap["OP_MLS"]   = OpMls;
  89       OpMap["OP_MUL_N"] = OpMulN;
  90       OpMap["OP_MULL_N"]= OpMullN;
  91       OpMap["OP_MLA_N"] = OpMlaN;
  92       OpMap["OP_MLS_N"] = OpMlsN;
  93       OpMap["OP_MUL_LN"]= OpMulLane;
  94       OpMap["OP_MULL_LN"] = OpMullLane;
  95       OpMap["OP_MLA_LN"]= OpMlaLane;
  96       OpMap["OP_MLS_LN"]= OpMlsLane;
  97       OpMap["OP_EQ"]    = OpEq;
  98       OpMap["OP_GE"]    = OpGe;
  99       OpMap["OP_LE"]    = OpLe;
 100       OpMap["OP_GT"]    = OpGt;
 101       OpMap["OP_LT"]    = OpLt;
 102       OpMap["OP_NEG"]   = OpNeg;
 103       OpMap["OP_NOT"]   = OpNot;
 104       OpMap["OP_AND"]   = OpAnd;
 105       OpMap["OP_OR"]    = OpOr;
 106       OpMap["OP_XOR"]   = OpXor;
 107       OpMap["OP_ANDN"]  = OpAndNot;
 108       OpMap["OP_ORN"]   = OpOrNot;
 109       OpMap["OP_CAST"]  = OpCast;
 110       OpMap["OP_CONC"]  = OpConcat;
 111       OpMap["OP_HI"]    = OpHi;
 112       OpMap["OP_LO"]    = OpLo;
 113       OpMap["OP_DUP"]   = OpDup;
 114       OpMap["OP_DUP_LN"] = OpDupLane;
 115       OpMap["OP_SEL"]   = OpSelect;
 116       OpMap["OP_REV16"] = OpRev16;
 117       OpMap["OP_REV32"] = OpRev32;
 118       OpMap["OP_REV64"] = OpRev64;
 119       OpMap["OP_REINT"] = OpReinterpret;
 120
 121       Record *SI = R.getClass("SInst");
 122       Record *II = R.getClass("IInst");
 123       Record *WI = R.getClass("WInst");
 124       ClassMap[SI] = ClassS;
 125       ClassMap[II] = ClassI;
 126       ClassMap[WI] = ClassW;
 127     }
 128
 129     // run - Emit arm_neon.h.inc
 130     void run(raw_ostream &o);
 131
 132     // runHeader - Emit all the __builtin prototypes used in arm_neon.h
 133     void runHeader(raw_ostream &o);
 134   };
 135
 136 } // End llvm namespace
 137
 138 #endif