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 "llvm/TableGen/Record.h"
  20 #include "llvm/TableGen/TableGenBackend.h"
  21 #include "llvm/ADT/DenseMap.h"
  22 #include "llvm/ADT/StringMap.h"
  23
  24 enum OpKind {
  25   OpNone,
  26   OpAdd,
  27   OpAddl,
  28   OpAddw,
  29   OpSub,
  30   OpSubl,
  31   OpSubw,
  32   OpMul,
  33   OpMla,
  34   OpMlal,
  35   OpMls,
  36   OpMlsl,
  37   OpMulN,
  38   OpMlaN,
  39   OpMlsN,
  40   OpMlalN,
  41   OpMlslN,
  42   OpMulLane,
  43   OpMullLane,
  44   OpMlaLane,
  45   OpMlsLane,
  46   OpMlalLane,
  47   OpMlslLane,
  48   OpQDMullLane,
  49   OpQDMlalLane,
  50   OpQDMlslLane,
  51   OpQDMulhLane,
  52   OpQRDMulhLane,
  53   OpEq,
  54   OpGe,
  55   OpLe,
  56   OpGt,
  57   OpLt,
  58   OpNeg,
  59   OpNot,
  60   OpAnd,
  61   OpOr,
  62   OpXor,
  63   OpAndNot,
  64   OpOrNot,
  65   OpCast,
  66   OpConcat,
  67   OpDup,
  68   OpDupLane,
  69   OpHi,
  70   OpLo,
  71   OpSelect,
  72   OpRev16,
  73   OpRev32,
  74   OpRev64,
  75   OpReinterpret,
  76   OpAbdl,
  77   OpAba,
  78   OpAbal
  79 };
  80
  81 enum ClassKind {
  82   ClassNone,
  83   ClassI,           // generic integer instruction, e.g., "i8" suffix
  84   ClassS,           // signed/unsigned/poly, e.g., "s8", "u8" or "p8" suffix
  85   ClassW,           // width-specific instruction, e.g., "8" suffix
  86   ClassB            // bitcast arguments with enum argument to specify type
  87 };
  88
  89 namespace llvm {
  90
  91   class NeonEmitter : public TableGenBackend {
  92     RecordKeeper &Records;
  93     StringMap<OpKind> OpMap;
  94     DenseMap<Record*, ClassKind> ClassMap;
  95
  96   public:
  97     NeonEmitter(RecordKeeper &R) : Records(R) {
  98       OpMap["OP_NONE"]  = OpNone;
  99       OpMap["OP_ADD"]   = OpAdd;
 100       OpMap["OP_ADDL"]  = OpAddl;
 101       OpMap["OP_ADDW"]  = OpAddw;
 102       OpMap["OP_SUB"]   = OpSub;
 103       OpMap["OP_SUBL"]  = OpSubl;
 104       OpMap["OP_SUBW"]  = OpSubw;
 105       OpMap["OP_MUL"]   = OpMul;
 106       OpMap["OP_MLA"]   = OpMla;
 107       OpMap["OP_MLAL"]  = OpMlal;
 108       OpMap["OP_MLS"]   = OpMls;
 109       OpMap["OP_MLSL"]  = OpMlsl;
 110       OpMap["OP_MUL_N"] = OpMulN;
 111       OpMap["OP_MLA_N"] = OpMlaN;
 112       OpMap["OP_MLS_N"] = OpMlsN;
 113       OpMap["OP_MLAL_N"] = OpMlalN;
 114       OpMap["OP_MLSL_N"] = OpMlslN;
 115       OpMap["OP_MUL_LN"]= OpMulLane;
 116       OpMap["OP_MULL_LN"] = OpMullLane;
 117       OpMap["OP_MLA_LN"]= OpMlaLane;
 118       OpMap["OP_MLS_LN"]= OpMlsLane;
 119       OpMap["OP_MLAL_LN"] = OpMlalLane;
 120       OpMap["OP_MLSL_LN"] = OpMlslLane;
 121       OpMap["OP_QDMULL_LN"] = OpQDMullLane;
 122       OpMap["OP_QDMLAL_LN"] = OpQDMlalLane;
 123       OpMap["OP_QDMLSL_LN"] = OpQDMlslLane;
 124       OpMap["OP_QDMULH_LN"] = OpQDMulhLane;
 125       OpMap["OP_QRDMULH_LN"] = OpQRDMulhLane;
 126       OpMap["OP_EQ"]    = OpEq;
 127       OpMap["OP_GE"]    = OpGe;
 128       OpMap["OP_LE"]    = OpLe;
 129       OpMap["OP_GT"]    = OpGt;
 130       OpMap["OP_LT"]    = OpLt;
 131       OpMap["OP_NEG"]   = OpNeg;
 132       OpMap["OP_NOT"]   = OpNot;
 133       OpMap["OP_AND"]   = OpAnd;
 134       OpMap["OP_OR"]    = OpOr;
 135       OpMap["OP_XOR"]   = OpXor;
 136       OpMap["OP_ANDN"]  = OpAndNot;
 137       OpMap["OP_ORN"]   = OpOrNot;
 138       OpMap["OP_CAST"]  = OpCast;
 139       OpMap["OP_CONC"]  = OpConcat;
 140       OpMap["OP_HI"]    = OpHi;
 141       OpMap["OP_LO"]    = OpLo;
 142       OpMap["OP_DUP"]   = OpDup;
 143       OpMap["OP_DUP_LN"] = OpDupLane;
 144       OpMap["OP_SEL"]   = OpSelect;
 145       OpMap["OP_REV16"] = OpRev16;
 146       OpMap["OP_REV32"] = OpRev32;
 147       OpMap["OP_REV64"] = OpRev64;
 148       OpMap["OP_REINT"] = OpReinterpret;
 149       OpMap["OP_ABDL"]  = OpAbdl;
 150       OpMap["OP_ABA"]   = OpAba;
 151       OpMap["OP_ABAL"]  = OpAbal;
 152
 153       Record *SI = R.getClass("SInst");
 154       Record *II = R.getClass("IInst");
 155       Record *WI = R.getClass("WInst");
 156       ClassMap[SI] = ClassS;
 157       ClassMap[II] = ClassI;
 158       ClassMap[WI] = ClassW;
 159     }
 160
 161     // run - Emit arm_neon.h.inc
 162     void run(raw_ostream &o);
 163
 164     // runHeader - Emit all the __builtin prototypes used in arm_neon.h
 165     void runHeader(raw_ostream &o);
 166
 167     // runTests - Emit tests for all the Neon intrinsics.
 168     void runTests(raw_ostream &o);
 169
 170   private:
 171     void emitIntrinsic(raw_ostream &OS, Record *R);
 172   };
 173
 174 } // End llvm namespace
 175
 176 #endif